Home
last modified time | relevance | path

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

/f-stack/dpdk/drivers/net/octeontx2/
H A Dotx2_lookup.c66 otx2_nix_ptypes_set(struct rte_eth_dev *eth_dev, uint32_t ptype_mask) in otx2_nix_ptypes_set() argument
70 if (ptype_mask) { in otx2_nix_ptypes_set()
H A Dotx2_ethdev.h560 int otx2_nix_ptypes_set(struct rte_eth_dev *eth_dev, uint32_t ptype_mask);
/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_lpm.c553 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in lpm_check_ptype() local
555 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in lpm_check_ptype()
561 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in lpm_check_ptype()
H A Dl3fwd_em.c523 uint32_t ptype_mask = RTE_PTYPE_L3_MASK | RTE_PTYPE_L4_MASK; in em_check_ptype() local
525 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in em_check_ptype()
531 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in em_check_ptype()
/f-stack/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c403 const __m256i ptype_mask = in _ice_recv_raw_pkts_vec_avx2() local
406 _mm256_and_si256(raw_desc6_7, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
408 _mm256_and_si256(raw_desc4_5, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
436 _mm256_and_si256(raw_desc2_3, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
438 _mm256_and_si256(raw_desc0_1, ptype_mask); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c378 const __m512i ptype_mask = in _ice_recv_raw_pkts_vec_avx512() local
386 _mm512_and_si512(raw_desc4_7, ptype_mask); in _ice_recv_raw_pkts_vec_avx512()
388 _mm512_and_si512(raw_desc0_3, ptype_mask); in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx_vec_sse.c240 const __m128i ptype_mask = _mm_set_epi16(ICE_RX_FLEX_DESC_PTYPE_M, 0, in ice_rx_desc_to_ptype_v() local
248 ptype_all = _mm_and_si128(ptype_all, ptype_mask); in ice_rx_desc_to_ptype_v()
/f-stack/dpdk/examples/ip_fragmentation/
H A Dmain.c652 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in check_ptype() local
654 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in check_ptype()
660 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c871 const __m256i ptype_mask = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() local
874 _mm256_and_si256(raw_desc6_7, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
876 _mm256_and_si256(raw_desc4_5, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
904 _mm256_and_si256(raw_desc2_3, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
906 _mm256_and_si256(raw_desc0_1, ptype_mask); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c877 const __m512i ptype_mask = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local
880 _mm512_and_si512(raw_desc4_7, ptype_mask); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
907 _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 = _mm_set_epi16(0, IAVF_RX_FLEX_DESC_PTYPE_M, in flex_desc_to_ptype_v() local
374 ptype_all = _mm_and_si128(ptype_all, ptype_mask); in flex_desc_to_ptype_v()
/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c160 uint32x4_t ptype_mask = vdupq_n_u32((uint32_t)pkt_type_mask); in desc_to_ptype_v() local
178 ptype_mask); in desc_to_ptype_v()
H A Dixgbe_rxtx_vec_sse.c265 __m128i ptype_mask = _mm_set_epi32( in desc_to_ptype_v() local
285 ptype_mask); in desc_to_ptype_v()
H A Dixgbe_rxtx.c1374 ixgbe_rxd_pkt_info_to_pkt_type(uint32_t pkt_info, uint16_t ptype_mask) in ixgbe_rxd_pkt_info_to_pkt_type() argument
1380 pkt_info = (pkt_info >> IXGBE_PACKET_TYPE_SHIFT) & ptype_mask; in ixgbe_rxd_pkt_info_to_pkt_type()
/f-stack/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()
/f-stack/dpdk/lib/librte_ethdev/
H A Drte_ethdev.c3302 rte_eth_dev_get_supported_ptypes(uint16_t port_id, uint32_t ptype_mask, in rte_eth_dev_get_supported_ptypes() argument
3318 if (all_ptypes[i] & ptype_mask) { in rte_eth_dev_get_supported_ptypes()
3328 rte_eth_dev_set_ptypes(uint16_t port_id, uint32_t ptype_mask, in rte_eth_dev_set_ptypes() argument
3358 if (ptype_mask == 0) { in rte_eth_dev_set_ptypes()
3360 ptype_mask); in rte_eth_dev_set_ptypes()
3364 unused_mask = ptype_mask; in rte_eth_dev_set_ptypes()
3366 uint32_t mask = ptype_mask & valid_ptype_masks[i]; in rte_eth_dev_set_ptypes()
3391 if (ptype_mask & all_ptypes[i]) { in rte_eth_dev_set_ptypes()
3404 return (*dev->dev_ops->dev_ptypes_set)(dev, ptype_mask); in rte_eth_dev_set_ptypes()
H A Drte_ethdev_driver.h252 uint32_t ptype_mask);
H A Drte_ethdev.h3081 int rte_eth_dev_get_supported_ptypes(uint16_t port_id, uint32_t ptype_mask,
3117 int rte_eth_dev_set_ptypes(uint16_t port_id, uint32_t ptype_mask,
/f-stack/dpdk/examples/l3fwd-power/
H A Dmain.c2199 uint32_t ptype_mask = RTE_PTYPE_L3_MASK; in check_ptype() local
2201 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, NULL, 0); in check_ptype()
2207 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
/f-stack/dpdk/app/test-pmd/
H A Dcmdline.c16517 uint32_t ptype_mask = RTE_PTYPE_L2_MASK; in cmd_show_port_supported_ptypes_parsed() local
16522 ret = rte_eth_dev_get_supported_ptypes(port_id, ptype_mask, NULL, 0); in cmd_show_port_supported_ptypes_parsed()
16526 while (ptype_mask != RSVD_PTYPE_MASK) { in cmd_show_port_supported_ptypes_parsed()
16528 switch (ptype_mask) { in cmd_show_port_supported_ptypes_parsed()
16555 ptype_mask, ptypes, in cmd_show_port_supported_ptypes_parsed()
16568 ptype_mask <<= 4; in cmd_show_port_supported_ptypes_parsed()
16686 cmdline_fixed_string_t ptype_mask; member
16706 ptype_mask, "ptype_mask");
16722 uint32_t ptype_mask = res->mask; in cmd_set_port_ptypes_parsed() local
16734 ret = rte_eth_dev_set_ptypes(port_id, ptype_mask, ptypes, ret); in cmd_set_port_ptypes_parsed()