Home
last modified time | relevance | path

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

/dpdk/app/test/
H A Dtest_malloc.c84 if (!p1){ in test_align_overlap_per_lcore()
99 rte_free(p1); in test_align_overlap_per_lcore()
106 rte_free(p1); in test_align_overlap_per_lcore()
134 rte_free(p1); in test_align_overlap_per_lcore()
155 if (!p1){ in test_reordered_free_per_lcore()
202 rte_free(p1); in test_reordered_free_per_lcore()
207 rte_free(p1); in test_reordered_free_per_lcore()
213 rte_free(p1); in test_reordered_free_per_lcore()
297 if (!p1) in test_multi_alloc_statistics()
299 rte_free(p1); in test_multi_alloc_statistics()
[all …]
/dpdk/lib/ip_frag/
H A Dip_frag_internal.c288 struct ip_frag_pkt *p1, *p2; in ip_frag_lookup() local
308 p1 = IP_FRAG_TBL_POS(tbl, sig1); in ip_frag_lookup()
312 if (p1->key.key_len == IPV4_KEYLEN) in ip_frag_lookup()
319 p1, i, assoc, in ip_frag_lookup()
320 p1[i].key.src_dst[0], p1[i].key.id, p1[i].start); in ip_frag_lookup()
328 p1, i, assoc, in ip_frag_lookup()
329 IPv6_KEY_BYTES(p1[i].key.src_dst), p1[i].key.id, p1[i].start); in ip_frag_lookup()
331 if (ip_frag_key_cmp(key, &p1[i].key) == 0) in ip_frag_lookup()
332 return p1 + i; in ip_frag_lookup()
335 else if (max_cycles + p1[i].start < tms) in ip_frag_lookup()
[all …]
/dpdk/examples/multi_process/client_server_mp/mp_client/
H A Dclient.c168 uint16_t p1 = ports->id[i]; in configure_output_ports() local
170 output_ports[p1] = p2; in configure_output_ports()
171 output_ports[p2] = p1; in configure_output_ports()
173 configure_tx_buffer(p1, MBQ_CAPACITY); in configure_output_ports()
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_neon.h624 uint8_t *p0, *p1, *p2, *p3; in rxq_cq_process_v() local
637 p1 = p0 + (pkts_n - pos > 1) * sizeof(struct mlx5_cqe); in rxq_cq_process_v()
638 p2 = p1 + (pkts_n - pos > 2) * sizeof(struct mlx5_cqe); in rxq_cq_process_v()
645 c1 = vld1q_u64((uint64_t *)(p1 + 48)); in rxq_cq_process_v()
733 :[p3]"r"(p3), [p2]"r"(p2), [p1]"r"(p1), [p0]"r"(p0), in rxq_cq_process_v()
793 elts[pos + 1]->port = container_of(p1, struct mlx5_cqe, in rxq_cq_process_v()
812 (container_of(p1, struct mlx5_cqe, in rxq_cq_process_v()
831 rte_be_to_cpu_64(container_of(p1, in rxq_cq_process_v()
852 (p1, struct mlx5_cqe, in rxq_cq_process_v()
H A Dmlx5_rxtx_vec_sse.h601 unsigned int p1, p2, p3; in rxq_cq_process_v() local
627 p1 = _mm_extract_epi16(p, 1); in rxq_cq_process_v()
629 &cq[pos + p1].sop_drop_qpn); in rxq_cq_process_v()
665 cqe_tmp2 = _mm_load_si128((__m128i *)&cq[pos + p1]); in rxq_cq_process_v()
669 cqe_tmp2 = _mm_loadu_si128((__m128i *)&cq[pos + p1].csum); in rxq_cq_process_v()
673 cqe_tmp2 = _mm_loadl_epi64((__m128i *)&cq[pos + p1].rsvd4[2]); in rxq_cq_process_v()
741 pkts[pos + p1]->port = cq[pos + p1].user_index_low; in rxq_cq_process_v()
754 ts = rte_be_to_cpu_64(cq[pos + p1].timestamp); in rxq_cq_process_v()
767 rte_be_to_cpu_64(cq[pos + p1].timestamp)); in rxq_cq_process_v()
784 (cq[pos + p1].flow_table_metadata) & mask; in rxq_cq_process_v()
H A Dmlx5_rxtx_vec_altivec.h889 unsigned int p1, p2, p3; in rxq_cq_process_v() local
942 p1 = (unsigned int)((__vector unsigned short)p)[1]; in rxq_cq_process_v()
945 &cq[pos + p1].sop_drop_qpn, 0LL}; in rxq_cq_process_v()
1023 &cq[pos + p1].pkt_info; in rxq_cq_process_v()
1029 (signed int const *)&cq[pos + p1].csum); in rxq_cq_process_v()
1040 &cq[pos + p1].rsvd4[2], 0LL}; in rxq_cq_process_v()
1194 pkts[pos + p1]->port = cq[pos + p1].user_index_low; in rxq_cq_process_v()
1207 ts = rte_be_to_cpu_64(cq[pos + p1].timestamp); in rxq_cq_process_v()
1220 rte_be_to_cpu_64(cq[pos + p1].timestamp)); in rxq_cq_process_v()
/dpdk/examples/server_node_efd/node/
H A Dnode.c174 uint8_t p1 = info->id[i]; in configure_output_ports() local
177 output_ports[p1] = p2; in configure_output_ports()
178 output_ports[p2] = p1; in configure_output_ports()
180 configure_tx_buffer(p1, MBQ_CAPACITY); in configure_output_ports()
/dpdk/drivers/net/octeontx/base/
H A Docteontx_io.h29 :[p1]"r"(addr) \
35 ::[x0]"r"(val0), [x1]"r"(val1), [p1]"r"(addr) \
/dpdk/drivers/mempool/octeontx/
H A Docteontx_fpavf.h66 :[p1]"r"(addr) \
72 ::[x0]"r"(val0), [x1]"r"(val1), [p1]"r"(addr) \
/dpdk/lib/security/
H A Drte_security.c20 #define RTE_PTR_CHAIN3_OR_ERR_RET(p1, p2, p3, retval, last_retval) do { \ argument
21 RTE_PTR_OR_ERR_RET(p1, retval); \
22 RTE_PTR_OR_ERR_RET(p1->p2, retval); \
23 RTE_PTR_OR_ERR_RET(p1->p2->p3, last_retval); \
/dpdk/drivers/event/octeontx/
H A Dssovf_evdev.h103 :[p1]"r"(addr) \
109 ::[x0]"r"(val0), [x1]"r"(val1), [p1]"r"(addr) \
/dpdk/drivers/common/cnxk/
H A Droc_io.h29 : [p1] "r"(addr)); \
36 [x1] "r"(val1), [p1] "r"(addr)); \
/dpdk/drivers/net/thunderx/base/
H A Dnicvf_plat.h66 : [p1]"r"(addr) \
/dpdk/lib/hash/
H A Drte_cmp_arm64.h15 : [p1]"r"(key1) in rte_hash_k16_cmp_eq()
/dpdk/lib/vhost/
H A Dvhost.h646 static __rte_always_inline int guest_page_addrcmp(const void *p1, in guest_page_addrcmp() argument
649 const struct guest_page *page1 = (const struct guest_page *)p1; in guest_page_addrcmp()
660 static __rte_always_inline int guest_page_rangecmp(const void *p1, const void *p2) in guest_page_rangecmp() argument
662 const struct guest_page *page1 = (const struct guest_page *)p1; in guest_page_rangecmp()
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c58 uintptr_t p0, p1; in i40e_rxq_rearm() local
71 p1 = (uintptr_t)&mb1->rearm_data; in i40e_rxq_rearm()
72 *(uint64_t *)p1 = rxq->mbuf_initializer; in i40e_rxq_rearm()
/dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx_vec.c294 uintptr_t p0, p1; in fm10k_rxq_rearm() local
304 p1 = (uintptr_t)&mb1->rearm_data; in fm10k_rxq_rearm()
305 *(uint64_t *)p1 = rxq->mbuf_initializer; in fm10k_rxq_rearm()
/dpdk/drivers/event/sw/
H A Dsw_evdev_selftest.c2450 const int p1 = 1; in inflight_counts() local
2464 err = rte_event_port_link(evdev, t->port[p1], &t->qid[0], NULL, 1); in inflight_counts()
2535 if (stats.port_inflight[p1] != QID1_NUM) { in inflight_counts()
2549 uint32_t deq_pkts = rte_event_dequeue_burst(evdev, t->port[p1], events, in inflight_counts()
2557 if (stats.port_inflight[p1] != QID1_NUM) { in inflight_counts()
2563 err = rte_event_enqueue_burst(evdev, t->port[p1], &release_ev, in inflight_counts()
2579 if (stats.port_inflight[p1] != 0) { in inflight_counts()
/dpdk/app/test-bbdev/
H A Dtest_bbdev_perf.c1431 double I, Q, p0, p1, llr_, b[qm], log_syml_prob[qam]; in gen_qm8_llr() local
1497 p1 = -999999; in gen_qm8_llr()
1501 p1 = maxstar(p1, log_syml_prob[m]); in gen_qm8_llr()
1506 llr_ = p0 - p1; in gen_qm8_llr()
1528 double I, Q, p0, p1, llr_, b[qm], log_syml_prob[qam]; in gen_qm6_llr() local
1562 p1 = -999999; in gen_qm6_llr()
1566 p1 = maxstar(p1, log_syml_prob[m]); in gen_qm6_llr()
1571 llr_ = p0 - p1; in gen_qm6_llr()
1618 p1 = -999999; in gen_qm4_llr()
1622 p1 = maxstar(p1, log_syml_prob[m]); in gen_qm4_llr()
[all …]
/dpdk/doc/guides/sample_app_ug/
H A Dl2_forward_event.rst369 like p0--->p1, p1--->p2, p2--->p0.
426 like p0--->p1, p1--->p2, p2--->p0.
/dpdk/lib/eal/linux/
H A Deal_memory.c497 const struct hugepage_file *p1 = a; in cmp_physaddr() local
501 const struct hugepage_file *p1 = b; in cmp_physaddr()
504 if (p1->physaddr < p2->physaddr) in cmp_physaddr()
506 else if (p1->physaddr > p2->physaddr) in cmp_physaddr()
/dpdk/drivers/net/ngbe/base/
H A Dngbe_dummy.h17 #define TUP1 TUP(p1)
/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_flow.c627 uint16_t p0, p1; in port_mask_to_range() local
634 p1 = p0 | ~port_mask; in port_mask_to_range()
640 *port1 = p1; in port_mask_to_range()
/dpdk/drivers/net/txgbe/base/
H A Dtxgbe_dummy.h17 #define TUP1 TUP(p1)
/dpdk/drivers/net/cnxk/
H A Dcn10k_rx.h1142 void *p1 = in cn10k_nix_recv_pkts_vector() local
1149 rte_prefetch0(p1); in cn10k_nix_recv_pkts_vector()