Home
last modified time | relevance | path

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

123

/dpdk/drivers/net/ice/base/
H A Dice_flow.c1114 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1174 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1191 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1211 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1215 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1219 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1223 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1231 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1239 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
1247 ice_and_bitmap(params->ptypes, params->ptypes, in ice_flow_proc_seg_hdrs()
[all …]
H A Dice_parser.h103 ice_declare_bitmap(ptypes, ICE_FLOW_PTYPE_MAX);
H A Dice_parser.c498 ice_set_bit(rslt->ptype, prof->ptypes); in ice_parser_profile_init()
544 if (ice_is_bit_set(prof->ptypes, i)) in ice_parser_profile_dump()
H A Dice_flex_pipe.h66 ice_add_prof(struct ice_hw *hw, enum ice_block blk, u64 id, u8 ptypes[],
H A Dice_flex_pipe.c2605 *ptg = hw->blk[blk].xlt1.ptypes[ptype].ptg; in ice_ptg_find_ptype()
2653 if (ptype == (p - hw->blk[blk].xlt1.ptypes)) { in ice_ptg_remove_ptype()
2663 hw->blk[blk].xlt1.ptypes[ptype].next_ptype = NULL; in ice_ptg_remove_ptype()
2709 hw->blk[blk].xlt1.ptypes[ptype].next_ptype = in ice_ptg_add_mv_ptype()
2712 &hw->blk[blk].xlt1.ptypes[ptype]; in ice_ptg_add_mv_ptype()
2714 hw->blk[blk].xlt1.ptypes[ptype].ptg = ptg; in ice_ptg_add_mv_ptype()
4076 ice_free(hw, hw->blk[i].xlt1.ptypes); in ice_free_hw_tbls()
4134 ice_memset(xlt1->ptypes, 0, xlt1->count * sizeof(*xlt1->ptypes), in ice_clear_hw_tbls()
4201 xlt1->ptypes = (struct ice_ptg_ptype *) in ice_init_hw_tbls()
4204 if (!xlt1->ptypes) in ice_init_hw_tbls()
[all …]
/dpdk/lib/node/
H A Dethdev_rx.c148 uint32_t ptypes[MAX_PTYPES]; in ethdev_ptype_setup() local
152 rc = rte_eth_dev_get_supported_ptypes(port, RTE_PTYPE_L3_MASK, ptypes, in ethdev_ptype_setup()
155 if (ptypes[i] & RTE_PTYPE_L3_IPV4) in ethdev_ptype_setup()
157 if (ptypes[i] & RTE_PTYPE_L3_IPV6) in ethdev_ptype_setup()
/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_avx2.c74 __m256i ptype_idx, ptypes, is_tunnel; in recv_burst_vec_avx2() local
214 ptypes = _mm256_i32gather_epi32((int *)bnxt_ptype_table, in recv_burst_vec_avx2()
276 mbuf01 = _mm256_blend_epi32(mbuf01, ptypes, 0x11); in recv_burst_vec_avx2()
278 _mm256_srli_si256(ptypes, 4), 0x11); in recv_burst_vec_avx2()
280 _mm256_srli_si256(ptypes, 8), 0x11); in recv_burst_vec_avx2()
282 _mm256_srli_si256(ptypes, 12), 0x11); in recv_burst_vec_avx2()
/dpdk/drivers/net/netvsc/
H A Dhn_rndis.c953 uint32_t ptypes; in hn_rndis_get_ptypes() local
964 ptypes = RTE_PTYPE_L2_ETHER; in hn_rndis_get_ptypes()
967 ptypes |= RTE_PTYPE_L3_IPV4; in hn_rndis_get_ptypes()
971 ptypes |= RTE_PTYPE_L4_TCP; in hn_rndis_get_ptypes()
975 ptypes |= RTE_PTYPE_L4_UDP; in hn_rndis_get_ptypes()
977 return ptypes; in hn_rndis_get_ptypes()
H A Dhn_vf.c467 const uint32_t *ptypes = NULL; in hn_vf_supported_ptypes() local
472 ptypes = (*vf_dev->dev_ops->dev_supported_ptypes_get)(vf_dev); in hn_vf_supported_ptypes()
475 return ptypes; in hn_vf_supported_ptypes()
/dpdk/examples/l3fwd/
H A Dl3fwd_lpm.c660 uint32_t ptypes[ret]; in lpm_check_ptype() local
662 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in lpm_check_ptype()
664 if (ptypes[i] & RTE_PTYPE_L3_IPV4) in lpm_check_ptype()
666 if (ptypes[i] & RTE_PTYPE_L3_IPV6) in lpm_check_ptype()
H A Dl3fwd_em.c474 uint32_t ptypes[ret]; in em_check_ptype() local
476 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in em_check_ptype()
478 switch (ptypes[i]) { in em_check_ptype()
/dpdk/drivers/net/cnxk/
H A Dcnxk_lookup.c17 static const uint32_t ptypes[] = { in cnxk_nix_supported_ptypes_get() local
54 return ptypes; in cnxk_nix_supported_ptypes_get()
/dpdk/examples/ip_fragmentation/
H A Dmain.c661 uint32_t ptypes[ret]; in check_ptype() local
663 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
665 if (ptypes[i] & RTE_PTYPE_L3_IPV4) in check_ptype()
667 if (ptypes[i] & RTE_PTYPE_L3_IPV6) in check_ptype()
/dpdk/drivers/net/ngbe/
H A Dngbe_ptypes.c97 static u32 ptypes[] = { in ngbe_get_supported_ptypes() local
117 return ptypes; in ngbe_get_supported_ptypes()
/dpdk/drivers/net/mvneta/
H A Dmvneta_ethdev.c200 static const uint32_t ptypes[] = { in mvneta_dev_supported_ptypes_get() local
209 return ptypes; in mvneta_dev_supported_ptypes_get()
/dpdk/drivers/net/mlx5/
H A Dmlx5_ethdev.c549 static const uint32_t ptypes[] = { in mlx5_dev_supported_ptypes_get() local
571 return ptypes; in mlx5_dev_supported_ptypes_get()
/dpdk/drivers/net/mlx4/
H A Dmlx4_ethdev.c939 static const uint32_t ptypes[] = { in mlx4_dev_supported_ptypes_get() local
967 return ptypes; in mlx4_dev_supported_ptypes_get()
/dpdk/drivers/net/thunderx/
H A Dnicvf_ethdev.c303 static uint32_t ptypes[32]; in nicvf_dev_supported_ptypes_get() local
323 memcpy(ptypes, ptypes_common, copied); in nicvf_dev_supported_ptypes_get()
325 memcpy((char *)ptypes + copied, ptypes_tunnel, in nicvf_dev_supported_ptypes_get()
330 memcpy((char *)ptypes + copied, &ptypes_end, sizeof(ptypes_end)); in nicvf_dev_supported_ptypes_get()
333 return ptypes; in nicvf_dev_supported_ptypes_get()
/dpdk/drivers/net/enetc/
H A Denetc_ethdev.c78 static const uint32_t ptypes[] = { in enetc_supported_ptypes_get() local
89 return ptypes; in enetc_supported_ptypes_get()
/dpdk/examples/l3fwd-power/
H A Dmain.c2243 uint32_t ptypes[ret]; in check_ptype() local
2245 ret = rte_eth_dev_get_supported_ptypes(portid, ptype_mask, ptypes, ret); in check_ptype()
2247 if (ptypes[i] & RTE_PTYPE_L3_IPV4) in check_ptype()
2250 if (ptypes[i] & RTE_PTYPE_L3_IPV6) in check_ptype()
/dpdk/drivers/net/nfp/
H A Dnfp_common.c788 static const uint32_t ptypes[] = { in nfp_net_supported_ptypes_get() local
798 return ptypes; in nfp_net_supported_ptypes_get()
/dpdk/drivers/net/pfe/
H A Dpfe_ethdev.c503 static const uint32_t ptypes[] = { in pfe_supported_ptypes_get() local
517 return ptypes; in pfe_supported_ptypes_get()
/dpdk/drivers/net/txgbe/
H A Dtxgbe_ptypes.c191 static u32 ptypes[] = { in txgbe_get_supported_ptypes() local
211 return ptypes; in txgbe_get_supported_ptypes()
/dpdk/drivers/net/enic/
H A Denic_ethdev.c510 static const uint32_t ptypes[] = { in enicpmd_dev_supported_ptypes_get() local
547 return ptypes; in enicpmd_dev_supported_ptypes_get()
/dpdk/drivers/net/ice/
H A Dice_hash.c1219 id = (u64)ice_find_first_bit(prof->ptypes, UINT16_MAX); in ice_hash_add_raw_cfg()
1357 id = (u64)ice_find_first_bit(prof->ptypes, 0xFFFF); in ice_hash_rem_raw_cfg()

123