| /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 | 336 __m128i ptype1 = _mm_unpackhi_epi64(descs[2], descs[3]); in desc_to_ptype_v() local
339 ptype1 = _mm_srli_epi64(ptype1, 30); in desc_to_ptype_v()
343 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 0)]; in desc_to_ptype_v()
344 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 | 373 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _recv_raw_pkts_vec_avx2() local
377 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _recv_raw_pkts_vec_avx2()
|
| H A D | i40e_rxtx_vec_avx512.c | 482 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _recv_raw_pkts_vec_avx512() local
493 0, 0, 0, ptype_tbl[ptype1], in _recv_raw_pkts_vec_avx512()
|
| /dpdk/drivers/net/ixgbe/ |
| H A D | ixgbe_rxtx_vec_sse.c | 137 __m128i ptype0, ptype1, vtag0, vtag1, csum, udp_csum_skip; in desc_to_olflags_v() local
196 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]); in desc_to_olflags_v()
200 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in desc_to_olflags_v()
294 __m128i ptype1 = _mm_unpacklo_epi32(descs[1], descs[3]); in desc_to_ptype_v() local
299 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in desc_to_ptype_v()
|
| H A D | ixgbe_rxtx_vec_neon.c | 244 uint32x4_t ptype1 = vzipq_u32(vreinterpretq_u32_u64(descs[1]), in desc_to_ptype_v() local
250 ptype0 = vzipq_u32(ptype0, ptype1).val[0]; in desc_to_ptype_v()
|
| /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 | 317 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _iavf_recv_raw_pkts_vec_avx2() local
322 mb0_1 = _mm256_insert_epi32(mb0_1, type_table[ptype1], 4); in _iavf_recv_raw_pkts_vec_avx2()
808 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
813 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 | 381 const uint8_t ptype1 = _mm256_extract_epi8(ptypes0_1, 24); in _iavf_recv_raw_pkts_vec_avx512() local
387 0, 0, 0, type_table[ptype1], in _iavf_recv_raw_pkts_vec_avx512()
928 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
934 0, 0, 0, type_table[ptype1], in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
|
| /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
97 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]); in fm10k_desc_to_olflags_v()
101 ptype0 = _mm_unpacklo_epi32(ptype0, ptype1); in fm10k_desc_to_olflags_v()
|
| /dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_avx2.c | 372 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _ice_recv_raw_pkts_vec_avx2() local
377 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 | 456 const uint16_t ptype1 = _mm256_extract_epi16(ptypes0_1, 9); in _ice_recv_raw_pkts_vec_avx512() local
467 0, 0, 0, ptype_tbl[ptype1], in _ice_recv_raw_pkts_vec_avx512()
|