Home
last modified time | relevance | path

Searched refs:np (Results 1 – 18 of 18) sorted by relevance

/dpdk/lib/ring/
H A Drte_ring_hts_elem_pvt.h60 union __rte_ring_hts_pos np, op; in __rte_ring_hts_move_prod_head() local
93 np.pos.tail = op.pos.tail; in __rte_ring_hts_move_prod_head()
94 np.pos.head = op.pos.head + n; in __rte_ring_hts_move_prod_head()
102 &op.raw, np.raw, in __rte_ring_hts_move_prod_head()
118 union __rte_ring_hts_pos np, op; in __rte_ring_hts_move_cons_head() local
148 np.pos.tail = op.pos.tail; in __rte_ring_hts_move_cons_head()
149 np.pos.head = op.pos.head + n; in __rte_ring_hts_move_cons_head()
157 &op.raw, np.raw, in __rte_ring_hts_move_cons_head()
/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_tm.c320 struct tm_node *np; in tm_node_pipe_id() local
324 TAILQ_FOREACH(np, nl, node) { in tm_node_pipe_id()
2105 struct tm_node *np, in pipe_profile_build() argument
2237 struct tm_node *ns, *np; in pipe_profiles_generate() local
2434 np->shaper_profile; in subport_profile_build()
2548 TAILQ_FOREACH(np, nl, node) { in hierarchy_commit_check()
2857 np->weight = weight; in update_pipe_weight()
3056 struct tm_node *np, in update_pipe_rate() argument
3090 np->shaper_profile = sp; in update_pipe_rate()
3344 struct tm_node *np, in read_pipe_stats() argument
[all …]
H A Drte_eth_softnic_cli.c360 struct rte_tm_node_params np; in cmd_tmgr_node() local
365 memset(&np, 0, sizeof(struct rte_tm_node_params)); in cmd_tmgr_node()
366 np.shaper_profile_id = RTE_TM_SHAPER_PROFILE_ID_NONE; in cmd_tmgr_node()
367 np.nonleaf.n_sp_priorities = 1; in cmd_tmgr_node()
435 np.shaper_profile_id = RTE_TM_SHAPER_PROFILE_ID_NONE; in cmd_tmgr_node()
437 if (softnic_parser_read_uint32(&np.shaper_profile_id, tokens[2]) != 0) { in cmd_tmgr_node()
460 np.shared_shaper_id = &shared_shaper_id; in cmd_tmgr_node()
461 np.n_shared_shapers = 1; in cmd_tmgr_node()
475 if (softnic_parser_read_uint32(&np.nonleaf.n_sp_priorities, tokens[2]) != 0) { in cmd_tmgr_node()
499 &np, in cmd_tmgr_node()
/dpdk/lib/ethdev/
H A Drte_class_eth.c71 uint16_t id, nc, np, nf, i, c, p, f; in eth_representor_cmp() local
90 np = eth_da.nb_ports > 0 ? eth_da.nb_ports : 1; in eth_representor_cmp()
94 for (i = 0; i < nc * np * nf; ++i) { in eth_representor_cmp()
95 c = i / (np * nf); in eth_representor_cmp()
96 p = (i / nf) % np; in eth_representor_cmp()
/dpdk/drivers/bus/dpaa/base/qbman/
H A Dqman.c1978 np->fqd_link = be24_to_cpu(np->fqd_link); in qman_query_fq_np()
1979 np->odp_seq = be16_to_cpu(np->odp_seq); in qman_query_fq_np()
1980 np->orp_nesn = be16_to_cpu(np->orp_nesn); in qman_query_fq_np()
1987 np->ics_surp = be16_to_cpu(np->ics_surp); in qman_query_fq_np()
1988 np->byte_cnt = be32_to_cpu(np->byte_cnt); in qman_query_fq_np()
1989 np->frm_cnt = be24_to_cpu(np->frm_cnt); in qman_query_fq_np()
1990 np->ra1_sfdr = be16_to_cpu(np->ra1_sfdr); in qman_query_fq_np()
1991 np->ra2_sfdr = be16_to_cpu(np->ra2_sfdr); in qman_query_fq_np()
1992 np->od1_sfdr = be16_to_cpu(np->od1_sfdr); in qman_query_fq_np()
1993 np->od2_sfdr = be16_to_cpu(np->od2_sfdr); in qman_query_fq_np()
[all …]
/dpdk/app/test-pmd/
H A Dcmdline_tm.c1647 struct rte_tm_node_params np; in cmd_add_port_tm_nonleaf_node_parsed() local
1688 if (np.n_shared_shapers) { in cmd_add_port_tm_nonleaf_node_parsed()
1696 np.stats_mask = res->stats_mask; in cmd_add_port_tm_nonleaf_node_parsed()
1701 &np, &error); in cmd_add_port_tm_nonleaf_node_parsed()
1812 struct rte_tm_node_params np; in cmd_add_port_tm_nonleaf_node_pmode_parsed() local
1852 if (np.n_shared_shapers) { in cmd_add_port_tm_nonleaf_node_pmode_parsed()
1867 &np, &error); in cmd_add_port_tm_nonleaf_node_pmode_parsed()
1976 struct rte_tm_node_params np; in cmd_add_port_tm_leaf_node_parsed() local
2018 if (np.n_shared_shapers) { in cmd_add_port_tm_leaf_node_parsed()
2025 np.leaf.cman = res->cman_mode; in cmd_add_port_tm_leaf_node_parsed()
[all …]
/dpdk/lib/acl/
H A Dacl_run_avx512.c78 xmm_t cp, cr, np, nr; in resolve_mcle8_avx512x1() local
98 np = _mm_loadu_si128((const xmm_t *)(pri + mn)); in resolve_mcle8_avx512x1()
100 msk = _mm_cmpgt_epi32_mask(cp, np); in resolve_mcle8_avx512x1()
102 cp = _mm_mask_mov_epi32(np, msk, cp); in resolve_mcle8_avx512x1()
H A Dacl_run_avx512x16.h253 __m512i cp, cr, np, nr; in resolve_mcgt8_avx512x1() local
273 np = _mm512_maskz_loadu_epi32(cm, pri + mi); in resolve_mcgt8_avx512x1()
275 sm = _mm512_cmpgt_epi32_mask(cp, np); in resolve_mcgt8_avx512x1()
277 cp = _mm512_mask_mov_epi32(np, sm, cp); in resolve_mcgt8_avx512x1()
H A Dacl_run_avx512_common.h411 _T_simd cp, cr, np, nr, mch; in _F_() local
435 np = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, pri, in _F_()
438 m = _M_I_(cmpgt_epi32_mask)(cp, np); in _F_()
440 cp = _M_I_(mask_mov_epi32)(np, m, cp); in _F_()
/dpdk/lib/bpf/
H A Dbpf_load_elf.c274 struct rte_bpf_prm np; in bpf_load_elf() local
284 np = prm[0]; in bpf_load_elf()
285 np.ins = sd->d_buf; in bpf_load_elf()
286 np.nb_ins = sd->d_size / sizeof(struct ebpf_insn); in bpf_load_elf()
287 bpf = rte_bpf_load(&np); in bpf_load_elf()
/dpdk/lib/ipsec/
H A Diph.h20 remove_esph(char *np, char *op, uint32_t hlen) in remove_esph() argument
24 for (i = hlen; i-- != 0; np[i] = op[i]) in remove_esph()
32 insert_esph(char *np, char *op, uint32_t hlen) in insert_esph() argument
37 np[i] = op[i]; in insert_esph()
H A Desp_inb.c524 char *np, *op; in trs_process_step2() local
530 np = tun_process_step2(mb, ml, hlen, adj, tofs, tlen, sqn); in trs_process_step2()
533 remove_esph(np, op, hlen); in trs_process_step2()
534 return np; in trs_process_step2()
641 char *np; in trs_process() local
673 np = trs_process_step2(mb[i], ml[i], hl[i], cofs, in trs_process()
675 update_trs_l3hdr(sa, np + l2, mb[i]->pkt_len, in trs_process()
H A Desp_outb.c348 uint8_t np; in outb_trs_pkt_prepare() local
402 np = update_trs_l3hdr(sa, ph + l2len, mb->pkt_len - sqh_len, l2len, in outb_trs_pkt_prepare()
425 espt->next_proto = np; in outb_trs_pkt_prepare()
/dpdk/drivers/common/dpaax/
H A Ddpaa_of.c552 static const void *of_get_mac_addr(const struct device_node *np, in of_get_mac_addr() argument
555 return of_get_property(np, name, NULL); in of_get_mac_addr()
576 const void *of_get_mac_address(const struct device_node *np) in of_get_mac_address() argument
580 addr = of_get_mac_addr(np, "mac-address"); in of_get_mac_address()
584 addr = of_get_mac_addr(np, "local-mac-address"); in of_get_mac_address()
588 return of_get_mac_addr(np, "address"); in of_get_mac_address()
H A Ddpaa_of.h135 const void *of_get_mac_address(const struct device_node *np);
/dpdk/drivers/net/pfe/
H A Dpfe_ethdev.c935 const struct device_node *np; in pmd_pfe_probe() local
974 np = of_find_compatible_node(NULL, NULL, "fsl,pfe"); in pmd_pfe_probe()
975 if (!np) { in pmd_pfe_probe()
981 addr = of_get_address(np, 0, &cbus_size, NULL); in pmd_pfe_probe()
986 cbus_addr = of_translate_address(np, addr); in pmd_pfe_probe()
992 addr = of_get_address(np, 1, &ddr_size, NULL); in pmd_pfe_probe()
998 g_pfe->ddr_phys_baseaddr = of_translate_address(np, addr); in pmd_pfe_probe()
1019 prop = of_get_property(np, "fsl,pfe-num-interfaces", &size); in pmd_pfe_probe()
1039 pfe_get_gemac_if_proprties(g_pfe, np, ii, interface_count, in pmd_pfe_probe()
/dpdk/drivers/net/mlx5/linux/
H A Dmlx5_os.c1722 unsigned int np, i; in mlx5_device_bond_pci_match() local
1739 if (!np) in mlx5_device_bond_pci_match()
1748 for (i = 1; i <= np; ++i) { in mlx5_device_bond_pci_match()
1897 unsigned int np = 0; in mlx5_os_pci_probe_pf() local
1998 if (!np) in mlx5_os_pci_probe_pf()
2002 if (bd >= 0 && !np) { in mlx5_os_pci_probe_pf()
2011 sizeof(struct mlx5_dev_spawn_data) * (np ? np : nd), in mlx5_os_pci_probe_pf()
2019 if (bd >= 0 || np > 1) { in mlx5_os_pci_probe_pf()
2028 MLX5_ASSERT(np); in mlx5_os_pci_probe_pf()
2031 list[ns].max_port = np; in mlx5_os_pci_probe_pf()
[all …]
/dpdk/drivers/bus/dpaa/include/
H A Dfsl_qman.h1738 int qman_query_fq_np(struct qman_fq *fq, struct qm_mcr_queryfq_np *np);
2124 struct qm_mcr_queryfq_np np; in qman_poll_fq_for_init() local
2127 err = qman_query_fq_np(fq, &np); in qman_poll_fq_for_init()
2130 if ((np.state & QM_MCR_NP_STATE_MASK) == QM_MCR_NP_STATE_OOS) in qman_poll_fq_for_init()