Home
last modified time | relevance | path

Searched refs:ptype_mask (Results 1 – 21 of 21) sorted by relevance

/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c334 const __m256i ptype_mask = in _ice_recv_raw_pkts_vec_avx2() local
337 _mm256_and_si256(raw_desc6_7, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
339 _mm256_and_si256(raw_desc4_5, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
367 _mm256_and_si256(raw_desc2_3, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
369 _mm256_and_si256(raw_desc0_1, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_sse.c276 const __m128i ptype_mask = _mm_set_epi16(ICE_RX_FLEX_DESC_PTYPE_M, 0, in ice_rx_desc_to_ptype_v() local
284 ptype_all = _mm_and_si128(ptype_all, ptype_mask); in ice_rx_desc_to_ptype_v()
H A Dice_rxtx_vec_avx512.c430 const __m512i ptype_mask = in _ice_recv_raw_pkts_vec_avx512() local
438 _mm512_and_si512(raw_desc4_7, ptype_mask); in _ice_recv_raw_pkts_vec_avx512()
440 _mm512_and_si512(raw_desc0_3, ptype_mask); in _ice_recv_raw_pkts_vec_avx512()
/dpdk/examples/l3fwd/
H A Dl3fwd_lpm.c654 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in lpm_check_ptype() local
656 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in lpm_check_ptype()
662 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in lpm_check_ptype()
H A Dl3fwd_em.c468 uint32_t ptype_mask = RTE_PTYPE_L3_MASK | RTE_PTYPE_L4_MASK; in em_check_ptype() local
470 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in em_check_ptype()
476 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in em_check_ptype()
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c770 const __m256i ptype_mask = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
773 _mm256_and_si256(raw_desc6_7, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
775 _mm256_and_si256(raw_desc4_5, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
803 _mm256_and_si256(raw_desc2_3, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
805 _mm256_and_si256(raw_desc0_1, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c891 const __m512i ptype_mask = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
894 _mm512_and_si512(raw_desc4_7, ptype_mask); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
923 _mm512_and_si512(raw_desc0_3, ptype_mask); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
H A Diavf_rxtx_vec_sse.c366 const __m128i ptype_mask = in flex_desc_to_ptype_v() local
376 ptype_all = _mm_and_si128(ptype_all, ptype_mask); in flex_desc_to_ptype_v()
/dpdk/examples/ip_fragmentation/
H A Dmain.c655 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in check_ptype() local
657 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in check_ptype()
663 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c241 uint32x4_t ptype_mask = vdupq_n_u32((uint32_t)pkt_type_mask); in desc_to_ptype_v() local
259 ptype_mask); in desc_to_ptype_v()
H A Dixgbe_rxtx_vec_sse.c286 __m128i ptype_mask = _mm_set_epi32( in desc_to_ptype_v() local
306 ptype_mask); in desc_to_ptype_v()
H A Dixgbe_rxtx.c1405 ixgbe_rxd_pkt_info_to_pkt_type(uint32_t pkt_info, uint16_t ptype_mask) in ixgbe_rxd_pkt_info_to_pkt_type() argument
1411 pkt_info = (pkt_info >> IXGBE_PACKET_TYPE_SHIFT) & ptype_mask; in ixgbe_rxd_pkt_info_to_pkt_type()
/dpdk/drivers/net/cnxk/
H A Dcn9k_ethdev.c120 cn9k_nix_ptypes_set(struct rte_eth_dev *eth_dev, uint32_t ptype_mask) in cn9k_nix_ptypes_set() argument
124 if (ptype_mask) { in cn9k_nix_ptypes_set()
H A Dcn10k_ethdev.c120 cn10k_nix_ptypes_set(struct rte_eth_dev *eth_dev, uint32_t ptype_mask) in cn10k_nix_ptypes_set() argument
124 if (ptype_mask) { in cn10k_nix_ptypes_set()
/dpdk/lib/ethdev/
H A Drte_ethdev.c3174 rte_eth_dev_get_supported_ptypes(uint16_t port_id, uint32_t ptype_mask, in rte_eth_dev_get_supported_ptypes() argument
3198 if (all_ptypes[i] & ptype_mask) { in rte_eth_dev_get_supported_ptypes()
3208 rte_eth_dev_set_ptypes(uint16_t port_id, uint32_t ptype_mask, in rte_eth_dev_set_ptypes() argument
3242 if (ptype_mask == 0) { in rte_eth_dev_set_ptypes()
3244 ptype_mask); in rte_eth_dev_set_ptypes()
3248 unused_mask = ptype_mask; in rte_eth_dev_set_ptypes()
3250 uint32_t mask = ptype_mask & valid_ptype_masks[i]; in rte_eth_dev_set_ptypes()
3275 if (ptype_mask & all_ptypes[i]) { in rte_eth_dev_set_ptypes()
3288 return (*dev->dev_ops->dev_ptypes_set)(dev, ptype_mask); in rte_eth_dev_set_ptypes()
H A Dethdev_driver.h455 uint32_t ptype_mask);
H A Drte_ethdev.h3491 int rte_eth_dev_get_supported_ptypes(uint16_t port_id, uint32_t ptype_mask,
3523 int rte_eth_dev_set_ptypes(uint16_t port_id, uint32_t ptype_mask,
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_sse.h388 const __m128i ptype_mask = _mm_set1_epi32(0xfd06); in rxq_cq_to_ptype_oflags_v() local
449 ptype = _mm_and_si128(ptype, ptype_mask); in rxq_cq_to_ptype_oflags_v()
H A Dmlx5_rxtx_vec_altivec.h544 const __vector unsigned char ptype_mask = in rxq_cq_to_ptype_oflags_v()
654 (__vector unsigned long)ptype_mask); in rxq_cq_to_ptype_oflags_v()
/dpdk/examples/l3fwd-power/
H A Dmain.c2237 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in check_ptype() local
2239 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in check_ptype()
2245 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
/dpdk/app/test-pmd/
H A Dcmdline.c17351 uint32_t ptype_mask = RTE_PTYPE_L2_MASK; in cmd_show_port_supported_ptypes_parsed() local
17356 ret = rte_eth_dev_get_supported_ptypes(port_id, ptype_mask, NULL, 0); in cmd_show_port_supported_ptypes_parsed()
17360 while (ptype_mask != RSVD_PTYPE_MASK) { in cmd_show_port_supported_ptypes_parsed()
17362 switch (ptype_mask) { in cmd_show_port_supported_ptypes_parsed()
17389 ptype_mask, ptypes, in cmd_show_port_supported_ptypes_parsed()
17402 ptype_mask <<= 4; in cmd_show_port_supported_ptypes_parsed()
17606 cmdline_fixed_string_t ptype_mask; member
17626 ptype_mask, "ptype_mask");
17642 uint32_t ptype_mask = res->mask; in cmd_set_port_ptypes_parsed() local
17655 ret = rte_eth_dev_set_ptypes(port_id, ptype_mask, ptypes, ret); in cmd_set_port_ptypes_parsed()