Home
last modified time | relevance | path

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

/f-stack/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_avx2.c517 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _recv_raw_pkts_vec_avx2() local
554 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_bits); in _recv_raw_pkts_vec_avx2()
606 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
609 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
612 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
615 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_add_flags); in _recv_raw_pkts_vec_avx2()
640 rearm6 = _mm256_blend_epi32(mbuf_init, _mm256_slli_si256(mbuf_flags, 8), 0x04); in _recv_raw_pkts_vec_avx2()
641 rearm4 = _mm256_blend_epi32(mbuf_init, _mm256_slli_si256(mbuf_flags, 4), 0x04); in _recv_raw_pkts_vec_avx2()
642 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _recv_raw_pkts_vec_avx2()
643 rearm0 = _mm256_blend_epi32(mbuf_init, _mm256_srli_si256(mbuf_flags, 4), 0x04); in _recv_raw_pkts_vec_avx2()
[all …]
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c473 const __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _iavf_recv_raw_pkts_vec_avx2() local
497 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx2()
500 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2()
504 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2()
524 (_mm256_extracti128_si256(mbuf_flags, 1)); in _iavf_recv_raw_pkts_vec_avx2()
949 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
966 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1106 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1109 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1113 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
[all …]
H A Diavf_rxtx_vec_avx512.c468 const __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _iavf_recv_raw_pkts_vec_avx512() local
497 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx512()
500 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512()
504 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512()
524 (_mm256_extracti128_si256(mbuf_flags, 1)); in _iavf_recv_raw_pkts_vec_avx512()
959 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
976 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1121 _mm256_slli_si256(mbuf_flags, 8), in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1124 _mm256_slli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1128 _mm256_srli_si256(mbuf_flags, 4), in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
[all …]
/f-stack/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c481 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _ice_recv_raw_pkts_vec_avx2() local
498 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _ice_recv_raw_pkts_vec_avx2()
638 _mm256_slli_si256(mbuf_flags, 8), in _ice_recv_raw_pkts_vec_avx2()
641 _mm256_slli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx2()
643 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _ice_recv_raw_pkts_vec_avx2()
645 _mm256_srli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx2()
665 (_mm256_extracti128_si256(mbuf_flags, 1)); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c463 __m256i mbuf_flags = _mm256_or_si256(l3_l4_flags, in _ice_recv_raw_pkts_vec_avx512() local
481 mbuf_flags = _mm256_or_si256(mbuf_flags, fdir_flags); in _ice_recv_raw_pkts_vec_avx512()
622 _mm256_slli_si256(mbuf_flags, 8), in _ice_recv_raw_pkts_vec_avx512()
625 _mm256_slli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx512()
627 rearm2 = _mm256_blend_epi32(mbuf_init, mbuf_flags, 0x04); in _ice_recv_raw_pkts_vec_avx512()
629 _mm256_srli_si256(mbuf_flags, 4), in _ice_recv_raw_pkts_vec_avx512()
651 (_mm256_extracti128_si256(mbuf_flags, 1)); in _ice_recv_raw_pkts_vec_avx512()
/f-stack/dpdk/drivers/net/atlantic/
H A Datl_rxtx.c845 uint64_t mbuf_flags = 0; in atl_desc_to_offload_flags() local
853 mbuf_flags |= PKT_RX_IP_CKSUM_BAD; in atl_desc_to_offload_flags()
855 mbuf_flags |= PKT_RX_IP_CKSUM_GOOD; in atl_desc_to_offload_flags()
857 mbuf_flags |= PKT_RX_IP_CKSUM_UNKNOWN; in atl_desc_to_offload_flags()
863 mbuf_flags |= PKT_RX_L4_CKSUM_BAD; in atl_desc_to_offload_flags()
865 mbuf_flags |= PKT_RX_L4_CKSUM_GOOD; in atl_desc_to_offload_flags()
867 mbuf_flags |= PKT_RX_L4_CKSUM_UNKNOWN; in atl_desc_to_offload_flags()
870 return mbuf_flags; in atl_desc_to_offload_flags()
/f-stack/dpdk/drivers/net/sfc/
H A Dsfc_rx.c136 uint64_t mbuf_flags = 0; in sfc_efx_rx_desc_flags_to_offload_flags() local
140 mbuf_flags |= PKT_RX_IP_CKSUM_GOOD; in sfc_efx_rx_desc_flags_to_offload_flags()
143 mbuf_flags |= PKT_RX_IP_CKSUM_BAD; in sfc_efx_rx_desc_flags_to_offload_flags()
147 SFC_ASSERT((mbuf_flags & PKT_RX_IP_CKSUM_MASK) == in sfc_efx_rx_desc_flags_to_offload_flags()
156 mbuf_flags |= PKT_RX_L4_CKSUM_GOOD; in sfc_efx_rx_desc_flags_to_offload_flags()
160 mbuf_flags |= PKT_RX_L4_CKSUM_BAD; in sfc_efx_rx_desc_flags_to_offload_flags()
164 SFC_ASSERT((mbuf_flags & PKT_RX_L4_CKSUM_MASK) == in sfc_efx_rx_desc_flags_to_offload_flags()
169 return mbuf_flags; in sfc_efx_rx_desc_flags_to_offload_flags()
/f-stack/freebsd/netinet/
H A Dsctp_uio.h903 uint8_t mbuf_flags; member
H A Dsctputil.c252 sctp_clog.x.mb.mbuf_flags = (uint8_t)(SCTP_BUF_GET_FLAGS(m)); in sctp_log_mb()
/f-stack/tools/compat/include/netinet/
H A Dsctp_uio.h903 uint8_t mbuf_flags; member