| /f-stack/dpdk/drivers/net/i40e/ |
| H A D | i40e_rxtx_vec_altivec.c | 176 vector unsigned long ptype1 = vec_mergel(descs[2], descs[3]); in desc_to_ptype_v() local
179 ptype1 = vec_sr(ptype1, (vector unsigned long){30, 30}); in desc_to_ptype_v()
186 ptype_tbl[(*(vector unsigned char *)&ptype1)[0]]; in desc_to_ptype_v()
188 ptype_tbl[(*(vector unsigned char *)&ptype1)[8]]; in desc_to_ptype_v()
|
| H A D | i40e_rxtx_vec_sse.c | 334 __m128i ptype1 = _mm_unpackhi_epi64(descs[2], descs[3]); in desc_to_ptype_v() local
337 ptype1 = _mm_srli_epi64(ptype1, 30); in desc_to_ptype_v()
341 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 0)]; in desc_to_ptype_v()
342 rx_pkts[3]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 8)]; in desc_to_ptype_v()
|
| H A D | i40e_rxtx_vec_avx2.c | 477 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _recv_raw_pkts_vec_avx2() local
481 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _recv_raw_pkts_vec_avx2()
|
| /f-stack/dpdk/drivers/net/ixgbe/ |
| H A D | ixgbe_rxtx_vec_sse.c | 137 __m128i ptype0, ptype1, vtag0, vtag1, csum; in desc_to_olflags_v() local
186 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]); in desc_to_olflags_v()
190 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in desc_to_olflags_v()
273 __m128i ptype1 = _mm_unpacklo_epi32(descs[1], descs[3]); in desc_to_ptype_v() local
278 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in desc_to_ptype_v()
|
| H A D | ixgbe_rxtx_vec_neon.c | 163 uint32x4_t ptype1 = vzipq_u32(vreinterpretq_u32_u64(descs[1]), in desc_to_ptype_v() local
169 ptype0 = vzipq_u32(ptype0, ptype1).val[0]; in desc_to_ptype_v()
|
| /f-stack/dpdk/drivers/net/iavf/ |
| H A D | iavf_rxtx_vec_sse.c | 351 __m128i ptype1 = _mm_unpackhi_epi64(descs[2], descs[3]); in desc_to_ptype_v() local
354 ptype1 = _mm_srli_epi64(ptype1, 30); in desc_to_ptype_v()
358 rx_pkts[2]->packet_type = type_table[_mm_extract_epi8(ptype1, 0)]; in desc_to_ptype_v()
359 rx_pkts[3]->packet_type = type_table[_mm_extract_epi8(ptype1, 8)]; in desc_to_ptype_v()
|
| H A D | iavf_rxtx_vec_avx2.c | 433 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _iavf_recv_raw_pkts_vec_avx2() local
438 mb0_1 = _mm256_insert_epi32(mb0_1, type_table[ptype1], 4); in _iavf_recv_raw_pkts_vec_avx2()
909 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
914 mb0_1 = _mm256_insert_epi32(mb0_1, type_table[ptype1], 4); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
|
| H A D | iavf_rxtx_vec_avx512.c | 421 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _iavf_recv_raw_pkts_vec_avx512() local
427 0, 0, 0, type_table[ptype1], in _iavf_recv_raw_pkts_vec_avx512()
912 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
918 0, 0, 0, type_table[ptype1], in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
|
| /f-stack/dpdk/drivers/net/fm10k/ |
| H A D | fm10k_rxtx_vec.c | 47 __m128i ptype0, ptype1, vtag0, vtag1, eflag0, eflag1, cksumflag; in fm10k_desc_to_olflags_v() local
96 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]); in fm10k_desc_to_olflags_v()
100 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in fm10k_desc_to_olflags_v()
|
| /f-stack/dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_avx2.c | 441 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _ice_recv_raw_pkts_vec_avx2() local
446 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _ice_recv_raw_pkts_vec_avx2()
|
| H A D | ice_rxtx_vec_avx512.c | 404 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _ice_recv_raw_pkts_vec_avx512() local
415 0, 0, 0, ptype_tbl[ptype1], in _ice_recv_raw_pkts_vec_avx512()
|