Home
last modified time | relevance | path

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

/f-stack/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
95 rss_flags = _mm_srli_epi32(_mm_and_si128(flags_type, rss_mask), 9); in descs_to_mbufs()
111 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
115 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
119 GET_OL_FLAGS(rss_flags, index, errors, 2, ol_flags); in descs_to_mbufs()
123 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
107 rss_flags = vshrq_n_u32(vandq_u32(flags_type, rss_mask), 9); in descs_to_mbufs()
125 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
128 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
131 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()
/f-stack/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()
/f-stack/dpdk/drivers/net/bnx2x/
H A Dbnx2x_vfpf.h97 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.c6658 rte_bit_relaxed_set32(ECORE_RSS_MODE_REGULAR, &params.rss_flags); in bnx2x_config_rss_pf()
6661 rte_bit_relaxed_set32(ECORE_RSS_IPV4, &params.rss_flags); in bnx2x_config_rss_pf()
6662 rte_bit_relaxed_set32(ECORE_RSS_IPV4_TCP, &params.rss_flags); in bnx2x_config_rss_pf()
6663 rte_bit_relaxed_set32(ECORE_RSS_IPV6, &params.rss_flags); in bnx2x_config_rss_pf()
6664 rte_bit_relaxed_set32(ECORE_RSS_IPV6_TCP, &params.rss_flags); in bnx2x_config_rss_pf()
6666 rte_bit_relaxed_set32(ECORE_RSS_IPV4_UDP, &params.rss_flags); in bnx2x_config_rss_pf()
6669 rte_bit_relaxed_set32(ECORE_RSS_IPV6_UDP, &params.rss_flags); in bnx2x_config_rss_pf()
6684 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
/f-stack/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_neon.c116 const uint8x16_t rss_flags = { in desc_to_olflags_v() local
146 rss = vreinterpretq_u32_u8(vqtbl1q_u8(rss_flags, 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
277 rss = _mm_shuffle_epi8(rss_flags, desc_fltstat); in desc_to_olflags_v()
H A Di40e_rxtx_vec_avx2.c504 const __m256i rss_flags = _mm256_shuffle_epi8(rss_flags_shuf, in _recv_raw_pkts_vec_avx2() local
518 _mm256_or_si256(rss_flags, vlan_flags)); in _recv_raw_pkts_vec_avx2()
/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c111 const uint8x16_t rss_flags = { in desc_to_olflags_v() local
119 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(PKT_RX_FDIR, 0, 0, 0, in desc_to_olflags_v() local
192 ptype0 = _mm_shuffle_epi8(rss_flags, ptype0); in desc_to_olflags_v()
/f-stack/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
102 ptype0 = _mm_shuffle_epi8(rss_flags, ptype0); in fm10k_desc_to_olflags_v()
/f-stack/dpdk/drivers/net/iavf/
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()
H A Diavf_rxtx_vec_avx2.c460 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx2() local
474 _mm256_or_si256(rss_flags, vlan_flags)); in _iavf_recv_raw_pkts_vec_avx2()
H A Diavf_rxtx_vec_avx512.c455 const __m256i rss_flags = in _iavf_recv_raw_pkts_vec_avx512() local
469 _mm256_or_si256(rss_flags, vlan_flags)); in _iavf_recv_raw_pkts_vec_avx512()