Home
last modified time | relevance | path

Searched refs:rss_flags (Results 1 – 20 of 20) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_sse.c25 #define GET_OL_FLAGS(rss_flags, ol_index, errors, pi, ol_flags) \ argument
29 of = _mm_extract_epi32((rss_flags), (pi)) | \
74 __m128i t0, t1, flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
102 rss_flags = _mm_srli_epi32(_mm_and_si128(flags_type, rss_mask), 9); in descs_to_mbufs()
122 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
126 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
130 GET_OL_FLAGS(rss_flags, index, errors, 2, ol_flags); in descs_to_mbufs()
134 GET_OL_FLAGS(rss_flags, index, errors, 3, ol_flags); in descs_to_mbufs()
H A Dbnxt_rxtx_vec_neon.c25 #define GET_OL_FLAGS(rss_flags, ol_idx, errors, pi, ol_flags) \ argument
29 of = vgetq_lane_u32((rss_flags), (pi)) | \
81 uint32x4_t flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
115 rss_flags = vshrq_n_u32(vandq_u32(flags_type, rss_mask), 9); in descs_to_mbufs()
137 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
140 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
143 GET_OL_FLAGS(rss_flags, index, errors, 2, ol_flags); in descs_to_mbufs()
146 GET_OL_FLAGS(rss_flags, index, errors, 3, ol_flags); in descs_to_mbufs()
H A Dbnxt_rxtx_vec_avx2.c78 __m256i rss_flags; in recv_burst_vec_avx2() local
291 rss_flags = _mm256_and_si256(flags_type, rss_mask); in recv_burst_vec_avx2()
292 rss_flags = _mm256_srli_epi32(rss_flags, 9); in recv_burst_vec_avx2()
294 ol_flags = _mm256_or_si256(ol_flags, rss_flags); in recv_burst_vec_avx2()
/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c486 __m256i rss_flags = _mm256_shuffle_epi8(rss_shuffle, rss_types); in enic_noscatter_vec_recv_pkts() local
531 rss_flags = _mm256_or_si256(rss_flags, csum_flags); in enic_noscatter_vec_recv_pkts()
581 rss_flags = _mm256_or_si256(rss_flags, vlan_flags); in enic_noscatter_vec_recv_pkts()
688 rss_flags, 0x44); in enic_noscatter_vec_recv_pkts()
690 _mm256_slli_si256(rss_flags, 4), 0x44); in enic_noscatter_vec_recv_pkts()
692 _mm256_slli_si256(rss_flags, 8), 0x44); in enic_noscatter_vec_recv_pkts()
694 _mm256_srli_si256(rss_flags, 4), 0x44); in enic_noscatter_vec_recv_pkts()
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c344 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx2() local
358 _mm256_or_si256(rss_flags, vlan_flags)); in _iavf_recv_raw_pkts_vec_avx2()
844 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
856 _mm256_or_si256(rss_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c500 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx512() local
519 mbuf_flags = _mm256_or_si256(mbuf_flags, rss_flags); in _iavf_recv_raw_pkts_vec_avx512()
1066 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
1076 _mm256_or_si256(rss_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
H A Diavf_rxtx_vec_sse.c130 const __m128i rss_flags = _mm_set_epi8(0, 0, 0, 0, in desc_to_olflags_v() local
156 rss = _mm_shuffle_epi8(rss_flags, rss); in desc_to_olflags_v()
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c124 const __vector unsigned char rss_flags = (__vector unsigned char){ in desc_to_olflags_v()
152 rss = (__vector unsigned int)vec_perm(rss_flags, (__vector unsigned char){}, in desc_to_olflags_v()
H A Di40e_rxtx_vec_sse.c250 const __m128i rss_flags = _mm_set_epi8(0, 0, 0, 0, in desc_to_olflags_v() local
279 rss = _mm_shuffle_epi8(rss_flags, desc_fltstat); in desc_to_olflags_v()
H A Di40e_rxtx_vec_neon.c241 const uint8x16_t rss_flags = { in desc_to_olflags_v() local
271 rss = vreinterpretq_u32_u8(vqtbl1q_u8(rss_flags, in desc_to_olflags_v()
H A Di40e_rxtx_vec_avx2.c400 const __m256i rss_flags = _mm256_shuffle_epi8(rss_flags_shuf, in _recv_raw_pkts_vec_avx2() local
414 _mm256_or_si256(rss_flags, vlan_flags)); in _recv_raw_pkts_vec_avx2()
H A Di40e_rxtx_vec_avx512.c529 const __m256i rss_flags = _mm256_shuffle_epi8(rss_flags_shuf, in _recv_raw_pkts_vec_avx512() local
542 _mm256_or_si256(rss_flags, vlan_flags)); in _recv_raw_pkts_vec_avx512()
/dpdk/drivers/net/bnx2x/
H A Dbnx2x_vfpf.h95 uint32_t rss_flags; member
H A Dbnx2x_vfpf.c632 query->rss_flags = params->rss_flags; in bnx2x_vf_config_rss()
H A Decore_sp.c3498 if (ECORE_TEST_BIT(ECORE_RSS_MODE_DISABLED, &p->rss_flags)) in ecore_setup_rss()
3500 else if (ECORE_TEST_BIT(ECORE_RSS_MODE_REGULAR, &p->rss_flags)) in ecore_setup_rss()
3508 if (ECORE_TEST_BIT(ECORE_RSS_IPV4, &p->rss_flags)) in ecore_setup_rss()
3512 if (ECORE_TEST_BIT(ECORE_RSS_IPV4_TCP, &p->rss_flags)) in ecore_setup_rss()
3516 if (ECORE_TEST_BIT(ECORE_RSS_IPV4_UDP, &p->rss_flags)) in ecore_setup_rss()
3520 if (ECORE_TEST_BIT(ECORE_RSS_IPV6, &p->rss_flags)) in ecore_setup_rss()
3524 if (ECORE_TEST_BIT(ECORE_RSS_IPV6_TCP, &p->rss_flags)) in ecore_setup_rss()
3528 if (ECORE_TEST_BIT(ECORE_RSS_IPV6_UDP, &p->rss_flags)) in ecore_setup_rss()
3548 if (ECORE_TEST_BIT(ECORE_RSS_SET_SRCH, &p->rss_flags)) { in ecore_setup_rss()
H A Dbnx2x.c6662 rte_bit_relaxed_set32(ECORE_RSS_MODE_REGULAR, &params.rss_flags); in bnx2x_config_rss_pf()
6665 rte_bit_relaxed_set32(ECORE_RSS_IPV4, &params.rss_flags); in bnx2x_config_rss_pf()
6666 rte_bit_relaxed_set32(ECORE_RSS_IPV4_TCP, &params.rss_flags); in bnx2x_config_rss_pf()
6667 rte_bit_relaxed_set32(ECORE_RSS_IPV6, &params.rss_flags); in bnx2x_config_rss_pf()
6668 rte_bit_relaxed_set32(ECORE_RSS_IPV6_TCP, &params.rss_flags); in bnx2x_config_rss_pf()
6670 rte_bit_relaxed_set32(ECORE_RSS_IPV4_UDP, &params.rss_flags); in bnx2x_config_rss_pf()
6673 rte_bit_relaxed_set32(ECORE_RSS_IPV6_UDP, &params.rss_flags); in bnx2x_config_rss_pf()
6688 rte_bit_relaxed_set32(ECORE_RSS_SET_SRCH, &params.rss_flags); in bnx2x_config_rss_pf()
H A Decore_sp.h1152 uint32_t rss_flags; member
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c107 const uint8x16_t rss_flags = { in desc_to_olflags_v() local
171 ptype = vqtbl1q_u8(rss_flags, ptype); in desc_to_olflags_v()
H A Dixgbe_rxtx_vec_sse.c151 const __m128i rss_flags = _mm_set_epi8(RTE_MBUF_F_RX_FDIR, 0, 0, 0, in desc_to_olflags_v() local
204 ptype0 = _mm_shuffle_epi8(rss_flags, ptype0); in desc_to_olflags_v()
/dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx_vec.c89 const __m128i rss_flags = _mm_set_epi8(0, 0, 0, 0, in fm10k_desc_to_olflags_v() local
103 ptype0 = _mm_shuffle_epi8(rss_flags, ptype0); in fm10k_desc_to_olflags_v()