Home
last modified time | relevance | path

Searched refs:vlan_flags (Results 1 – 19 of 19) sorted by relevance

/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_sse.c134 desc_to_olflags_v(__m128i descs[4], __m128i mbuf_init, uint8_t vlan_flags, in desc_to_olflags_v() argument
167 vlan_flags | PKT_RX_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
168 vlan_flags | PKT_RX_IP_CKSUM_BAD, in desc_to_olflags_v()
169 vlan_flags | PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
170 vlan_flags | PKT_RX_IP_CKSUM_GOOD, in desc_to_olflags_v()
343 uint8_t vlan_flags; in _recv_raw_pkts_vec() local
407 vlan_flags = rxq->vlan_flags & UINT8_MAX; in _recv_raw_pkts_vec()
480 desc_to_olflags_v(descs, mbuf_init, vlan_flags, &rx_pkts[pos]); in _recv_raw_pkts_vec()
H A Dixgbe_rxtx.h133 uint64_t vlan_flags; member
H A Dixgbe_rxtx.c1425 rx_desc_status_to_pkt_flags(uint32_t rx_status, uint64_t vlan_flags) in rx_desc_status_to_pkt_flags() argument
1434 pkt_flags = (rx_status & IXGBE_RXD_STAT_VP) ? vlan_flags : 0; in rx_desc_status_to_pkt_flags()
1501 uint64_t vlan_flags = rxq->vlan_flags; in ixgbe_rx_scan_hw_ring() local
1546 vlan_flags); in ixgbe_rx_scan_hw_ring()
1761 uint64_t vlan_flags; in ixgbe_recv_pkts() local
1769 vlan_flags = rxq->vlan_flags; in ixgbe_recv_pkts()
1879 pkt_flags = rx_desc_status_to_pkt_flags(staterr, vlan_flags); in ixgbe_recv_pkts()
1972 pkt_flags = rx_desc_status_to_pkt_flags(staterr, rxq->vlan_flags); in ixgbe_fill_cluster_head_buf()
H A Dixgbe_ethdev.c1962 rxq->vlan_flags = PKT_RX_VLAN | PKT_RX_VLAN_STRIPPED; in ixgbe_vlan_hw_strip_bitmap_set()
1965 rxq->vlan_flags = PKT_RX_VLAN; in ixgbe_vlan_hw_strip_bitmap_set()
/f-stack/dpdk/drivers/net/ice/
H A Dice_ethdev.c4080 uint8_t vlan_flags; in ice_vsi_config_vlan_stripping() local
4087 if ((vsi->info.vlan_flags & in ice_vsi_config_vlan_stripping()
4092 if ((vsi->info.vlan_flags & in ice_vsi_config_vlan_stripping()
4100 vlan_flags = ICE_AQ_VSI_VLAN_EMOD_STR_BOTH; in ice_vsi_config_vlan_stripping()
4102 vlan_flags = ICE_AQ_VSI_VLAN_EMOD_NOTHING; in ice_vsi_config_vlan_stripping()
4104 vsi->info.vlan_flags |= vlan_flags; in ice_vsi_config_vlan_stripping()
4574 uint8_t vlan_flags = 0; in ice_vsi_vlan_pvid_set() local
4588 vlan_flags = ICE_AQ_VSI_PVLAN_INSERT_PVID | in ice_vsi_vlan_pvid_set()
4593 vlan_flags |= ICE_AQ_VSI_VLAN_MODE_TAGGED; in ice_vsi_vlan_pvid_set()
4596 vlan_flags |= ICE_AQ_VSI_VLAN_MODE_UNTAGGED; in ice_vsi_vlan_pvid_set()
[all …]
/f-stack/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c578 __m256i vlan_flags = _mm256_permutevar8x32_epi32(vlan_shuffle, in enic_noscatter_vec_recv_pkts() local
581 rss_flags = _mm256_or_si256(rss_flags, vlan_flags); in enic_noscatter_vec_recv_pkts()
/f-stack/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c118 const vector unsigned char vlan_flags = (vector unsigned char){ in desc_to_olflags_v()
147 vlan0 = (vector unsigned int)vec_perm(vlan_flags, in desc_to_olflags_v()
H A Di40e_rxtx_vec_neon.c110 const uint8x16_t vlan_flags = { in desc_to_olflags_v() local
142 vlan0 = vreinterpretq_u32_u8(vqtbl1q_u8(vlan_flags, in desc_to_olflags_v()
H A Di40e_rxtx_vec_sse.c245 const __m128i vlan_flags = _mm_set_epi8(0, 0, 0, 0, in desc_to_olflags_v() local
274 vlan0 = _mm_shuffle_epi8(vlan_flags, vlan1); in desc_to_olflags_v()
H A Di40e_rxtx_vec_avx2.c501 const __m256i vlan_flags = _mm256_shuffle_epi8( in _recv_raw_pkts_vec_avx2() local
518 _mm256_or_si256(rss_flags, vlan_flags)); in _recv_raw_pkts_vec_avx2()
H A Di40e_ethdev.c5190 uint8_t vlan_flags = 0; in i40e_vsi_vlan_pvid_set() local
5204 vlan_flags |= I40E_AQ_VSI_PVLAN_INSERT_PVID | in i40e_vsi_vlan_pvid_set()
5209 vlan_flags |= I40E_AQ_VSI_PVLAN_MODE_TAGGED; in i40e_vsi_vlan_pvid_set()
5212 vlan_flags |= I40E_AQ_VSI_PVLAN_MODE_UNTAGGED; in i40e_vsi_vlan_pvid_set()
5216 vsi->info.port_vlan_flags |= vlan_flags; in i40e_vsi_vlan_pvid_set()
6095 uint8_t vlan_flags; in i40e_vsi_config_vlan_stripping() local
6114 vlan_flags = I40E_AQ_VSI_PVLAN_EMOD_STR_BOTH; in i40e_vsi_config_vlan_stripping()
6116 vlan_flags = I40E_AQ_VSI_PVLAN_EMOD_NOTHING; in i40e_vsi_config_vlan_stripping()
6120 vsi->info.port_vlan_flags |= vlan_flags; in i40e_vsi_config_vlan_stripping()
/f-stack/dpdk/drivers/net/txgbe/
H A Dtxgbe_rxtx.h306 uint64_t vlan_flags; member
H A Dtxgbe_rxtx.c1060 rx_desc_status_to_pkt_flags(uint32_t rx_status, uint64_t vlan_flags) in rx_desc_status_to_pkt_flags() argument
1070 vlan_flags & PKT_RX_VLAN_STRIPPED) in rx_desc_status_to_pkt_flags()
1071 ? vlan_flags : 0; in rx_desc_status_to_pkt_flags()
1171 rxq->vlan_flags); in txgbe_rx_scan_hw_ring()
1499 rxq->vlan_flags); in txgbe_recv_pkts()
1575 pkt_flags = rx_desc_status_to_pkt_flags(staterr, rxq->vlan_flags); in txgbe_fill_cluster_head_buf()
H A Dtxgbe_ethdev.c930 rxq->vlan_flags = PKT_RX_VLAN | PKT_RX_VLAN_STRIPPED; in txgbe_vlan_hw_strip_bitmap_set()
933 rxq->vlan_flags = PKT_RX_VLAN; in txgbe_vlan_hw_strip_bitmap_set()
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_sse.c125 const __m128i vlan_flags = _mm_set_epi8(0, 0, 0, 0, in desc_to_olflags_v() local
153 vlan0 = _mm_shuffle_epi8(vlan_flags, vlan1); in desc_to_olflags_v()
H A Diavf_rxtx_vec_avx2.c458 const __m256i vlan_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.c453 const __m256i vlan_flags = in _iavf_recv_raw_pkts_vec_avx512() local
469 _mm256_or_si256(rss_flags, vlan_flags)); in _iavf_recv_raw_pkts_vec_avx512()
/f-stack/dpdk/drivers/net/i40e/base/
H A Di40e_adminq_cmd.h1179 u8 vlan_flags; member
/f-stack/dpdk/drivers/net/ice/base/
H A Dice_adminq_cmd.h433 u8 vlan_flags; member