| /dpdk/drivers/net/hns3/ |
| H A D | hns3_rxtx_vec_neon.h | 151 uint16x8_t crc_adjust = { in hns3_recv_burst_vec() local 236 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb1), crc_adjust); in hns3_recv_burst_vec() 238 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb2), crc_adjust); in hns3_recv_burst_vec() 257 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb3), crc_adjust); in hns3_recv_burst_vec() 259 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb4), crc_adjust); in hns3_recv_burst_vec()
|
| /dpdk/drivers/net/iavf/ |
| H A D | iavf_rxtx_vec_sse.c | 403 __m128i crc_adjust = _mm_set_epi16( in _recv_raw_pkts_vec() local 552 pkt_mb4 = _mm_add_epi16(pkt_mb4, crc_adjust); in _recv_raw_pkts_vec() 553 pkt_mb3 = _mm_add_epi16(pkt_mb3, crc_adjust); in _recv_raw_pkts_vec() 580 pkt_mb2 = _mm_add_epi16(pkt_mb2, crc_adjust); in _recv_raw_pkts_vec() 581 pkt_mb1 = _mm_add_epi16(pkt_mb1, crc_adjust); in _recv_raw_pkts_vec() 652 __m128i crc_adjust = _mm_set_epi16 in _recv_raw_pkts_vec_flex_rxd() local 812 pkt_mb3 = _mm_add_epi16(pkt_mb3, crc_adjust); in _recv_raw_pkts_vec_flex_rxd() 813 pkt_mb2 = _mm_add_epi16(pkt_mb2, crc_adjust); in _recv_raw_pkts_vec_flex_rxd() 816 pkt_mb1 = _mm_add_epi16(pkt_mb1, crc_adjust); in _recv_raw_pkts_vec_flex_rxd() 817 pkt_mb0 = _mm_add_epi16(pkt_mb0, crc_adjust); in _recv_raw_pkts_vec_flex_rxd()
|
| H A D | iavf_rxtx_vec_avx2.c | 57 const __m256i crc_adjust = in _iavf_recv_raw_pkts_vec_avx2() local 274 mb6_7 = _mm256_add_epi16(mb6_7, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2() 275 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2() 310 mb2_3 = _mm256_add_epi16(mb2_3, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2() 311 mb0_1 = _mm256_add_epi16(mb0_1, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2() 557 const __m256i crc_adjust = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local 764 mb6_7 = _mm256_add_epi16(mb6_7, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 765 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 796 mb2_3 = _mm256_add_epi16(mb2_3, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 797 mb0_1 = _mm256_add_epi16(mb0_1, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
|
| H A D | iavf_rxtx_vec_avx512.c | 197 const __m512i crc_adjust = in _iavf_recv_raw_pkts_vec_avx512() local 340 mb4_7 = _mm512_add_epi32(mb4_7, crc_adjust); in _iavf_recv_raw_pkts_vec_avx512() 373 mb0_3 = _mm512_add_epi32(mb0_3, crc_adjust); in _iavf_recv_raw_pkts_vec_avx512() 746 const __m512i crc_adjust = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local 885 mb4_7 = _mm512_add_epi32(mb4_7, crc_adjust); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() 916 mb0_3 = _mm512_add_epi32(mb0_3, crc_adjust); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
|
| /dpdk/drivers/net/i40e/ |
| H A D | i40e_rxtx_vec_altivec.c | 210 __vector unsigned short crc_adjust = (__vector unsigned short){ in _recv_raw_pkts_vec() 344 (__vector unsigned short)pkt_mb4, crc_adjust); in _recv_raw_pkts_vec() 346 (__vector unsigned short)pkt_mb3, crc_adjust); in _recv_raw_pkts_vec() 382 (__vector unsigned short)pkt_mb2, crc_adjust); in _recv_raw_pkts_vec() 384 (__vector unsigned short)pkt_mb1, crc_adjust); in _recv_raw_pkts_vec()
|
| H A D | i40e_rxtx_vec_sse.c | 366 __m128i crc_adjust = _mm_set_epi16( in _recv_raw_pkts_vec() local 519 pkt_mb4 = _mm_add_epi16(pkt_mb4, crc_adjust); in _recv_raw_pkts_vec() 520 pkt_mb3 = _mm_add_epi16(pkt_mb3, crc_adjust); in _recv_raw_pkts_vec() 545 pkt_mb2 = _mm_add_epi16(pkt_mb2, crc_adjust); in _recv_raw_pkts_vec() 546 pkt_mb1 = _mm_add_epi16(pkt_mb1, crc_adjust); in _recv_raw_pkts_vec()
|
| H A D | i40e_rxtx_vec_neon.c | 363 uint16x8_t crc_adjust = { in _recv_raw_pkts_vec() local 484 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb4), crc_adjust); in _recv_raw_pkts_vec() 486 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb3), crc_adjust); in _recv_raw_pkts_vec() 488 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb2), crc_adjust); in _recv_raw_pkts_vec() 490 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb1), crc_adjust); in _recv_raw_pkts_vec()
|
| H A D | i40e_rxtx_vec_avx2.c | 142 const __m256i crc_adjust = _mm256_set_epi16( in _recv_raw_pkts_vec_avx2() local 336 mb6_7 = _mm256_add_epi16(mb6_7, crc_adjust); in _recv_raw_pkts_vec_avx2() 337 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _recv_raw_pkts_vec_avx2() 366 mb2_3 = _mm256_add_epi16(mb2_3, crc_adjust); in _recv_raw_pkts_vec_avx2() 367 mb0_1 = _mm256_add_epi16(mb0_1, crc_adjust); in _recv_raw_pkts_vec_avx2()
|
| H A D | i40e_rxtx_vec_avx512.c | 266 const __m512i crc_adjust = in _recv_raw_pkts_vec_avx512() local 460 mb4_7 = _mm512_add_epi32(mb4_7, crc_adjust); in _recv_raw_pkts_vec_avx512() 461 mb0_3 = _mm512_add_epi32(mb0_3, crc_adjust); in _recv_raw_pkts_vec_avx512()
|
| /dpdk/drivers/net/ixgbe/ |
| H A D | ixgbe_rxtx_vec_neon.c | 303 uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, in _recv_raw_pkts_vec() local 408 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb4), crc_adjust); in _recv_raw_pkts_vec() 410 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb3), crc_adjust); in _recv_raw_pkts_vec() 420 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb2), crc_adjust); in _recv_raw_pkts_vec() 422 tmp = vsubq_u16(vreinterpretq_u16_u8(pkt_mb1), crc_adjust); in _recv_raw_pkts_vec()
|
| H A D | ixgbe_rxtx_vec_sse.c | 346 __m128i crc_adjust = _mm_set_epi16( in _recv_raw_pkts_vec() local 525 pkt_mb4 = _mm_add_epi16(pkt_mb4, crc_adjust); in _recv_raw_pkts_vec() 526 pkt_mb3 = _mm_add_epi16(pkt_mb3, crc_adjust); in _recv_raw_pkts_vec() 539 pkt_mb2 = _mm_add_epi16(pkt_mb2, crc_adjust); in _recv_raw_pkts_vec() 540 pkt_mb1 = _mm_add_epi16(pkt_mb1, crc_adjust); in _recv_raw_pkts_vec()
|
| /dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_sse.c | 309 __m128i crc_adjust = _mm_set_epi16 in _ice_recv_raw_pkts_vec() local 469 pkt_mb3 = _mm_add_epi16(pkt_mb3, crc_adjust); in _ice_recv_raw_pkts_vec() 470 pkt_mb2 = _mm_add_epi16(pkt_mb2, crc_adjust); in _ice_recv_raw_pkts_vec() 473 pkt_mb1 = _mm_add_epi16(pkt_mb1, crc_adjust); in _ice_recv_raw_pkts_vec() 474 pkt_mb0 = _mm_add_epi16(pkt_mb0, crc_adjust); in _ice_recv_raw_pkts_vec()
|
| H A D | ice_rxtx_vec_avx2.c | 72 const __m256i crc_adjust = in _ice_recv_raw_pkts_vec_avx2() local 328 mb6_7 = _mm256_add_epi16(mb6_7, crc_adjust); in _ice_recv_raw_pkts_vec_avx2() 329 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _ice_recv_raw_pkts_vec_avx2() 360 mb2_3 = _mm256_add_epi16(mb2_3, crc_adjust); in _ice_recv_raw_pkts_vec_avx2() 361 mb0_1 = _mm256_add_epi16(mb0_1, crc_adjust); in _ice_recv_raw_pkts_vec_avx2()
|
| H A D | ice_rxtx_vec_avx512.c | 186 const __m512i crc_adjust = in _ice_recv_raw_pkts_vec_avx512() local 423 mb4_7 = _mm512_add_epi32(mb4_7, crc_adjust); in _ice_recv_raw_pkts_vec_avx512() 424 mb0_3 = _mm512_add_epi32(mb0_3, crc_adjust); in _ice_recv_raw_pkts_vec_avx512()
|