Home
last modified time | relevance | path

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

/dpdk/drivers/net/ice/
H A Dice_dcf_vf_representor.c262 vlan_offload.vlan_flags = in ice_dcf_vf_repr_vlan_offload_set()
266 vlan_offload.vlan_flags = in ice_dcf_vf_repr_vlan_offload_set()
270 if (vlan_offload.vlan_flags) { in ice_dcf_vf_repr_vlan_offload_set()
273 vlan_offload.vlan_flags |= in ice_dcf_vf_repr_vlan_offload_set()
311 vlan_offload.vlan_flags = in ice_dcf_vf_repr_vlan_pvid_set()
315 vlan_offload.vlan_flags = in ice_dcf_vf_repr_vlan_pvid_set()
321 vlan_offload.vlan_flags |= (VIRTCHNL_DCF_VLAN_TYPE_OUTER << in ice_dcf_vf_repr_vlan_pvid_set()
H A Dice_ethdev.c4851 uint8_t vlan_flags = 0; in ice_vsi_vlan_pvid_set() local
4865 vlan_flags = ICE_AQ_VSI_INNER_VLAN_INSERT_PVID | in ice_vsi_vlan_pvid_set()
4870 vlan_flags |= ICE_AQ_VSI_INNER_VLAN_TX_MODE_ACCEPTTAGGED; in ice_vsi_vlan_pvid_set()
4873 vlan_flags |= ICE_AQ_VSI_INNER_VLAN_TX_MODE_ACCEPTUNTAGGED; in ice_vsi_vlan_pvid_set()
4877 vsi->info.inner_vlan_flags |= vlan_flags; in ice_vsi_vlan_pvid_set()
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c86 uint8x16_t staterr, uint8_t vlan_flags, uint16_t udp_p_flag, in desc_to_olflags_v() argument
131 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_GOOD, in desc_to_olflags_v()
132 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_GOOD | RTE_MBUF_F_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
133 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_BAD, in desc_to_olflags_v()
134 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_BAD | RTE_MBUF_F_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
305 uint8_t vlan_flags; in _recv_raw_pkts_vec() local
341 vlan_flags = rxq->vlan_flags & UINT8_MAX; in _recv_raw_pkts_vec()
404 desc_to_olflags_v(sterr_tmp1, sterr_tmp2, staterr, vlan_flags, in _recv_raw_pkts_vec()
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
168 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_BAD | RTE_MBUF_F_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
169 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_BAD, in desc_to_olflags_v()
170 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_GOOD | RTE_MBUF_F_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
171 vlan_flags | RTE_MBUF_F_RX_IP_CKSUM_GOOD, in desc_to_olflags_v()
364 uint8_t vlan_flags; in _recv_raw_pkts_vec() local
443 vlan_flags = rxq->vlan_flags & UINT8_MAX; in _recv_raw_pkts_vec()
516 desc_to_olflags_v(descs, mbuf_init, vlan_flags, udp_p_flag, in _recv_raw_pkts_vec()
H A Dixgbe_rxtx.h135 uint64_t vlan_flags; member
H A Dixgbe_rxtx.c1456 rx_desc_status_to_pkt_flags(uint32_t rx_status, uint64_t vlan_flags) in rx_desc_status_to_pkt_flags() argument
1465 pkt_flags = (rx_status & IXGBE_RXD_STAT_VP) ? vlan_flags : 0; in rx_desc_status_to_pkt_flags()
1542 uint64_t vlan_flags = rxq->vlan_flags; in ixgbe_rx_scan_hw_ring() local
1587 vlan_flags); in ixgbe_rx_scan_hw_ring()
1804 uint64_t vlan_flags; in ixgbe_recv_pkts() local
1812 vlan_flags = rxq->vlan_flags; in ixgbe_recv_pkts()
1922 pkt_flags = rx_desc_status_to_pkt_flags(staterr, vlan_flags); in ixgbe_recv_pkts()
2017 pkt_flags = rx_desc_status_to_pkt_flags(staterr, rxq->vlan_flags); in ixgbe_fill_cluster_head_buf()
H A Dixgbe_ethdev.c1985 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN | RTE_MBUF_F_RX_VLAN_STRIPPED; in ixgbe_vlan_hw_strip_bitmap_set()
1988 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN; in ixgbe_vlan_hw_strip_bitmap_set()
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c342 const __m256i vlan_flags = in _iavf_recv_raw_pkts_vec_avx2() local
358 _mm256_or_si256(rss_flags, vlan_flags)); in _iavf_recv_raw_pkts_vec_avx2()
848 __m256i vlan_flags = _mm256_setzero_si256(); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
851 vlan_flags = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
856 _mm256_or_si256(rss_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1033 vlan_flags = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1039 (mbuf_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c496 const __m256i vlan_flags = in _iavf_recv_raw_pkts_vec_avx512() local
522 mbuf_flags = _mm256_or_si256(mbuf_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx512()
959 __m256i vlan_flags = _mm256_setzero_si256(); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
1071 vlan_flags = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1076 _mm256_or_si256(rss_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1282 vlan_flags = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1290 vlan_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
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()
/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()
/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_sse.c245 const __m128i vlan_flags = _mm_set_epi8(0, 0, 0, 0, in desc_to_olflags_v() local
276 vlan0 = _mm_shuffle_epi8(vlan_flags, vlan1); in desc_to_olflags_v()
H A Di40e_rxtx_vec_neon.c235 const uint8x16_t vlan_flags = { in desc_to_olflags_v() local
267 vlan0 = vreinterpretq_u32_u8(vqtbl1q_u8(vlan_flags, in desc_to_olflags_v()
H A Di40e_rxtx_vec_avx2.c397 const __m256i vlan_flags = _mm256_shuffle_epi8( 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.c526 const __m256i vlan_flags = in _recv_raw_pkts_vec_avx512() local
542 _mm256_or_si256(rss_flags, vlan_flags)); in _recv_raw_pkts_vec_avx512()
H A Di40e_ethdev.c5150 uint8_t vlan_flags = 0; in i40e_vsi_vlan_pvid_set() local
5164 vlan_flags |= I40E_AQ_VSI_PVLAN_INSERT_PVID | in i40e_vsi_vlan_pvid_set()
5169 vlan_flags |= I40E_AQ_VSI_PVLAN_MODE_TAGGED; in i40e_vsi_vlan_pvid_set()
5172 vlan_flags |= I40E_AQ_VSI_PVLAN_MODE_UNTAGGED; in i40e_vsi_vlan_pvid_set()
5176 vsi->info.port_vlan_flags |= vlan_flags; in i40e_vsi_vlan_pvid_set()
6056 uint8_t vlan_flags; in i40e_vsi_config_vlan_stripping() local
6075 vlan_flags = I40E_AQ_VSI_PVLAN_EMOD_STR_BOTH; in i40e_vsi_config_vlan_stripping()
6077 vlan_flags = I40E_AQ_VSI_PVLAN_EMOD_NOTHING; in i40e_vsi_config_vlan_stripping()
6081 vsi->info.port_vlan_flags |= vlan_flags; in i40e_vsi_config_vlan_stripping()
/dpdk/drivers/net/ngbe/
H A Dngbe_rxtx.h273 uint64_t vlan_flags; member
H A Dngbe_rxtx.c940 rx_desc_status_to_pkt_flags(uint32_t rx_status, uint64_t vlan_flags) in rx_desc_status_to_pkt_flags() argument
950 vlan_flags & RTE_MBUF_F_RX_VLAN_STRIPPED) in rx_desc_status_to_pkt_flags()
951 ? vlan_flags : 0; in rx_desc_status_to_pkt_flags()
1048 rxq->vlan_flags); in ngbe_rx_scan_hw_ring()
1370 rxq->vlan_flags); in ngbe_recv_pkts()
1441 pkt_flags = rx_desc_status_to_pkt_flags(staterr, rxq->vlan_flags); in ngbe_fill_cluster_head_buf()
H A Dngbe_ethdev.c714 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN | RTE_MBUF_F_RX_VLAN_STRIPPED; in ngbe_vlan_hw_strip_bitmap_set()
717 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN; in ngbe_vlan_hw_strip_bitmap_set()
/dpdk/drivers/net/txgbe/
H A Dtxgbe_rxtx.h311 uint64_t vlan_flags; member
H A Dtxgbe_rxtx.c1122 rx_desc_status_to_pkt_flags(uint32_t rx_status, uint64_t vlan_flags) in rx_desc_status_to_pkt_flags() argument
1132 vlan_flags & RTE_MBUF_F_RX_VLAN_STRIPPED) in rx_desc_status_to_pkt_flags()
1133 ? vlan_flags : 0; in rx_desc_status_to_pkt_flags()
1241 rxq->vlan_flags); in txgbe_rx_scan_hw_ring()
1569 rxq->vlan_flags); in txgbe_recv_pkts()
1645 pkt_flags = rx_desc_status_to_pkt_flags(staterr, rxq->vlan_flags); in txgbe_fill_cluster_head_buf()
H A Dtxgbe_ethdev.c1136 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN | RTE_MBUF_F_RX_VLAN_STRIPPED; in txgbe_vlan_hw_strip_bitmap_set()
1139 rxq->vlan_flags = RTE_MBUF_F_RX_VLAN; in txgbe_vlan_hw_strip_bitmap_set()
/dpdk/drivers/common/iavf/
H A Dvirtchnl.h1375 u16 vlan_flags; member
/dpdk/drivers/net/i40e/base/
H A Di40e_adminq_cmd.h1197 u8 vlan_flags; member