Home
last modified time | relevance | path

Searched refs:ptype_idx (Results 1 – 4 of 4) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_sse.c38 #define GET_DESC_FIELDS(rxcmp, rxcmp1, shuf_msk, ptype_idx, pi, ret) \ argument
47 ptype = bnxt_ptype_table[_mm_extract_epi32((ptype_idx), (pi))]; \
75 __m128i ptype_idx, is_tunnel; in descs_to_mbufs() local
85 ptype_idx = _mm_srli_epi32(_mm_and_si128(flags_type, flags_type_mask), in descs_to_mbufs()
92 ptype_idx = _mm_or_si128(ptype_idx, in descs_to_mbufs()
96 ptype_idx = _mm_or_si128(ptype_idx, in descs_to_mbufs()
139 GET_DESC_FIELDS(mm_rxcmp[0], mm_rxcmp1[0], shuf_msk, ptype_idx, 0, t0); in descs_to_mbufs()
142 GET_DESC_FIELDS(mm_rxcmp[1], mm_rxcmp1[1], shuf_msk, ptype_idx, 1, t0); in descs_to_mbufs()
145 GET_DESC_FIELDS(mm_rxcmp[2], mm_rxcmp1[2], shuf_msk, ptype_idx, 2, t0); in descs_to_mbufs()
148 GET_DESC_FIELDS(mm_rxcmp[3], mm_rxcmp1[3], shuf_msk, ptype_idx, 3, t0); in descs_to_mbufs()
H A Dbnxt_rxtx_vec_neon.c38 #define GET_DESC_FIELDS(rxcmp, rxcmp1, shuf_msk, ptype_idx, pkt_idx, ret) \ argument
49 ptype = bnxt_ptype_table[vgetq_lane_u32((ptype_idx), (pkt_idx))]; \
82 uint32x4_t tmp, ptype_idx, is_tunnel; in descs_to_mbufs() local
95 ptype_idx = vshrq_n_u32(vandq_u32(flags_type, flags_type_mask), in descs_to_mbufs()
105 ptype_idx = vorrq_u32(ptype_idx, in descs_to_mbufs()
109 ptype_idx = vorrq_u32(ptype_idx, in descs_to_mbufs()
151 GET_DESC_FIELDS(mm_rxcmp[0], mm_rxcmp1[0], shuf_msk, ptype_idx, 0, tmp); in descs_to_mbufs()
153 GET_DESC_FIELDS(mm_rxcmp[1], mm_rxcmp1[1], shuf_msk, ptype_idx, 1, tmp); in descs_to_mbufs()
155 GET_DESC_FIELDS(mm_rxcmp[2], mm_rxcmp1[2], shuf_msk, ptype_idx, 2, tmp); in descs_to_mbufs()
157 GET_DESC_FIELDS(mm_rxcmp[3], mm_rxcmp1[3], shuf_msk, ptype_idx, 3, tmp); in descs_to_mbufs()
H A Dbnxt_rxtx_vec_avx2.c74 __m256i ptype_idx, ptypes, is_tunnel; in recv_burst_vec_avx2() local
190 ptype_idx = _mm256_and_si256(flags_type, flags_type_mask); in recv_burst_vec_avx2()
191 ptype_idx = _mm256_srli_epi32(ptype_idx, in recv_burst_vec_avx2()
202 ptype_idx = _mm256_or_si256(ptype_idx, t0); in recv_burst_vec_avx2()
207 ptype_idx = _mm256_or_si256(ptype_idx, t0); in recv_burst_vec_avx2()
215 ptype_idx, sizeof(uint32_t)); in recv_burst_vec_avx2()
/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c596 __m256i ptype_idx = _mm256_or_si256(tcp_udp, ip4_ip6); in enic_noscatter_vec_recv_pkts() local
600 _mm256_shuffle_epi8(nonfrag_ptype_shuffle, ptype_idx); in enic_noscatter_vec_recv_pkts()
602 _mm256_shuffle_epi8(frag_ptype_shuffle, ptype_idx); in enic_noscatter_vec_recv_pkts()
619 _mm256_shuffle_epi8(tnl_l3_ptype_shuffle, ptype_idx); in enic_noscatter_vec_recv_pkts()