Home
last modified time | relevance | path

Searched refs:mbuf_flags (Results 1 – 8 of 8) sorted by relevance

/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_avx2.c413 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _recv_raw_pkts_vec_avx2() local
450 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_bits); in _recv_raw_pkts_vec_avx2()
502 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
505 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
508 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
511 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
536 rearm6 = _mm256_blend_epi32(mbuf_init, _mm256_slli_si256(mbuf_flags, 8), 0x04); in _recv_raw_pkts_vec_avx2()
537 rearm4 = _mm256_blend_epi32(mbuf_init, _mm256_slli_si256(mbuf_flags, 4), 0x04); in _recv_raw_pkts_vec_avx2()
538 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _recv_raw_pkts_vec_avx2()
539 rearm0 = _mm256_blend_epi32(mbuf_init, _mm256_srli_si256(mbuf_flags, 4), 0x04); in _recv_raw_pkts_vec_avx2()
[all …]
H A Di40e_rxtx_vec_avx512.c582 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_bits); in _recv_raw_pkts_vec_avx512()
651 mbuf_flags = in _recv_raw_pkts_vec_avx512()
652 _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx512()
656 mbuf_flags = in _recv_raw_pkts_vec_avx512()
657 _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx512()
661 mbuf_flags = in _recv_raw_pkts_vec_avx512()
662 _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx512()
666 mbuf_flags = in _recv_raw_pkts_vec_avx512()
667 _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx512()
696 (mbuf_init, mbuf_flags, 0x04); in _recv_raw_pkts_vec_avx512()
[all …]
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx512.c516 mbuf_flags = _mm256_or_si256(mbuf_flags, l3_l4_flags); in _iavf_recv_raw_pkts_vec_avx512()
519 mbuf_flags = _mm256_or_si256(mbuf_flags, rss_flags); in _iavf_recv_raw_pkts_vec_avx512()
522 mbuf_flags = _mm256_or_si256(mbuf_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx512()
554 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx512()
557 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512()
561 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512()
1081 mbuf_flags = _mm256_or_si256(mbuf_flags, l3_l4_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1084 mbuf_flags = _mm256_or_si256(mbuf_flags, rss_vlan_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1103 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1288 mbuf_flags = _mm256_or_si256 in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
[all …]
H A Diavf_rxtx_vec_avx2.c381 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx2()
384 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2()
388 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2()
408 (_mm256_extracti128_si256(mbuf_flags, 1)); in _iavf_recv_raw_pkts_vec_avx2()
876 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1038 mbuf_flags = _mm256_or_si256 in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1039 (mbuf_flags, vlan_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1094 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1097 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1101 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
[all …]
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c390 __m256i mbuf_flags = _mm256_set1_epi32(0); in _ice_recv_raw_pkts_vec_avx2() local
424 mbuf_flags = _mm256_or_si256(l3_l4_flags, in _ice_recv_raw_pkts_vec_avx2()
442 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _ice_recv_raw_pkts_vec_avx2()
584 _mm256_slli_si256(mbuf_flags, 8), in _ice_recv_raw_pkts_vec_avx2()
587 _mm256_slli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx2()
589 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _ice_recv_raw_pkts_vec_avx2()
591 _mm256_srli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx2()
611 (_mm256_extracti128_si256(mbuf_flags, 1)); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c494 __m256i mbuf_flags = _mm256_set1_epi32(0); in _ice_recv_raw_pkts_vec_avx512() local
527 mbuf_flags = _mm256_or_si256(l3_l4_flags, in _ice_recv_raw_pkts_vec_avx512()
547 mbuf_flags = _mm256_or_si256 in _ice_recv_raw_pkts_vec_avx512()
548 (mbuf_flags, fdir_flags); in _ice_recv_raw_pkts_vec_avx512()
550 mbuf_flags = in _ice_recv_raw_pkts_vec_avx512()
696 _mm256_slli_si256(mbuf_flags, 8), in _ice_recv_raw_pkts_vec_avx512()
699 _mm256_slli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx512()
701 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _ice_recv_raw_pkts_vec_avx512()
703 _mm256_srli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx512()
725 (_mm256_extracti128_si256(mbuf_flags, 1)); in _ice_recv_raw_pkts_vec_avx512()
/dpdk/drivers/net/atlantic/
H A Datl_rxtx.c840 uint64_t mbuf_flags = 0; in atl_desc_to_offload_flags() local
848 mbuf_flags |= RTE_MBUF_F_RX_IP_CKSUM_BAD; in atl_desc_to_offload_flags()
850 mbuf_flags |= RTE_MBUF_F_RX_IP_CKSUM_GOOD; in atl_desc_to_offload_flags()
852 mbuf_flags |= RTE_MBUF_F_RX_IP_CKSUM_UNKNOWN; in atl_desc_to_offload_flags()
858 mbuf_flags |= RTE_MBUF_F_RX_L4_CKSUM_BAD; in atl_desc_to_offload_flags()
860 mbuf_flags |= RTE_MBUF_F_RX_L4_CKSUM_GOOD; in atl_desc_to_offload_flags()
862 mbuf_flags |= RTE_MBUF_F_RX_L4_CKSUM_UNKNOWN; in atl_desc_to_offload_flags()
865 return mbuf_flags; in atl_desc_to_offload_flags()
/dpdk/drivers/net/sfc/
H A Dsfc_rx.c148 uint64_t mbuf_flags = 0; in sfc_efx_rx_desc_flags_to_offload_flags() local
152 mbuf_flags |= RTE_MBUF_F_RX_IP_CKSUM_GOOD; in sfc_efx_rx_desc_flags_to_offload_flags()
155 mbuf_flags |= RTE_MBUF_F_RX_IP_CKSUM_BAD; in sfc_efx_rx_desc_flags_to_offload_flags()
159 SFC_ASSERT((mbuf_flags & RTE_MBUF_F_RX_IP_CKSUM_MASK) == in sfc_efx_rx_desc_flags_to_offload_flags()
168 mbuf_flags |= RTE_MBUF_F_RX_L4_CKSUM_GOOD; in sfc_efx_rx_desc_flags_to_offload_flags()
172 mbuf_flags |= RTE_MBUF_F_RX_L4_CKSUM_BAD; in sfc_efx_rx_desc_flags_to_offload_flags()
176 SFC_ASSERT((mbuf_flags & RTE_MBUF_F_RX_L4_CKSUM_MASK) == in sfc_efx_rx_desc_flags_to_offload_flags()
181 return mbuf_flags; in sfc_efx_rx_desc_flags_to_offload_flags()