| /dpdk/app/test/ |
| H A D | test_malloc.c | 96 if (!p2){ in test_align_overlap_per_lcore()
107 rte_free(p2); in test_align_overlap_per_lcore()
135 rte_free(p2); in test_align_overlap_per_lcore()
203 rte_free(p2); in test_reordered_free_per_lcore()
209 rte_free(p2); in test_reordered_free_per_lcore()
212 rte_free(p2); in test_reordered_free_per_lcore()
217 rte_free(p2); in test_reordered_free_per_lcore()
224 rte_free(p2); in test_reordered_free_per_lcore()
228 rte_free(p2); in test_reordered_free_per_lcore()
318 if (!p2) in test_multi_alloc_statistics()
[all …]
|
| /dpdk/lib/ip_frag/ |
| H A D | ip_frag_internal.c | 288 struct ip_frag_pkt *p1, *p2; in ip_frag_lookup() local
309 p2 = IP_FRAG_TBL_POS(tbl, sig2); in ip_frag_lookup()
338 if (p2->key.key_len == IPV4_KEYLEN) in ip_frag_lookup()
345 p2, i, assoc, in ip_frag_lookup()
346 p2[i].key.src_dst[0], p2[i].key.id, p2[i].start); in ip_frag_lookup()
354 p2, i, assoc, in ip_frag_lookup()
355 IPv6_KEY_BYTES(p2[i].key.src_dst), p2[i].key.id, p2[i].start); in ip_frag_lookup()
357 if (ip_frag_key_cmp(key, &p2[i].key) == 0) in ip_frag_lookup()
358 return p2 + i; in ip_frag_lookup()
361 else if (max_cycles + p2[i].start < tms) in ip_frag_lookup()
[all …]
|
| /dpdk/examples/multi_process/client_server_mp/mp_client/ |
| H A D | client.c | 169 uint16_t p2 = ports->id[i+1]; in configure_output_ports() local
170 output_ports[p1] = p2; in configure_output_ports()
171 output_ports[p2] = p1; in configure_output_ports()
174 configure_tx_buffer(p2, MBQ_CAPACITY); in configure_output_ports()
|
| /dpdk/drivers/net/mlx5/ |
| H A D | mlx5_rxtx_vec_neon.h | 624 uint8_t *p0, *p1, *p2, *p3; in rxq_cq_process_v() local
638 p2 = p1 + (pkts_n - pos > 2) * sizeof(struct mlx5_cqe); in rxq_cq_process_v()
639 p3 = p2 + (pkts_n - pos > 3) * sizeof(struct mlx5_cqe); in rxq_cq_process_v()
643 c2 = vld1q_u64((uint64_t *)(p2 + 48)); in rxq_cq_process_v()
733 :[p3]"r"(p3), [p2]"r"(p2), [p1]"r"(p1), [p0]"r"(p0), in rxq_cq_process_v()
795 elts[pos + 2]->port = container_of(p2, struct mlx5_cqe, in rxq_cq_process_v()
817 (container_of(p2, struct mlx5_cqe, in rxq_cq_process_v()
834 rte_be_to_cpu_64(container_of(p2, in rxq_cq_process_v()
856 (p2, struct mlx5_cqe, in rxq_cq_process_v()
|
| H A D | mlx5_rxtx_vec_sse.h | 601 unsigned int p1, p2, p3; in rxq_cq_process_v() local
619 p2 = _mm_extract_epi16(p, 2); in rxq_cq_process_v()
621 &cq[pos + p2].sop_drop_qpn); in rxq_cq_process_v()
639 cqe_tmp1 = _mm_load_si128((__m128i *)&cq[pos + p2]); in rxq_cq_process_v()
643 cqe_tmp1 = _mm_loadu_si128((__m128i *)&cq[pos + p2].csum); in rxq_cq_process_v()
647 cqe_tmp1 = _mm_loadl_epi64((__m128i *)&cq[pos + p2].rsvd4[2]); in rxq_cq_process_v()
742 pkts[pos + p2]->port = cq[pos + p2].user_index_low; in rxq_cq_process_v()
757 ts = rte_be_to_cpu_64(cq[pos + p2].timestamp); in rxq_cq_process_v()
769 rte_be_to_cpu_64(cq[pos + p2].timestamp)); in rxq_cq_process_v()
787 (cq[pos + p2].flow_table_metadata) & mask; in rxq_cq_process_v()
|
| H A D | mlx5_rxtx_vec_altivec.h | 889 unsigned int p1, p2, p3; in rxq_cq_process_v() local
929 p2 = (unsigned int)((__vector unsigned short)p)[2]; in rxq_cq_process_v()
932 &cq[pos + p2].sop_drop_qpn, 0LL}; in rxq_cq_process_v()
962 &cq[pos + p2].pkt_info; in rxq_cq_process_v()
968 (signed int const *)&cq[pos + p2].csum); in rxq_cq_process_v()
980 &cq[pos + p2].rsvd4[2], 0LL}; in rxq_cq_process_v()
1195 pkts[pos + p2]->port = cq[pos + p2].user_index_low; in rxq_cq_process_v()
1210 ts = rte_be_to_cpu_64(cq[pos + p2].timestamp); in rxq_cq_process_v()
1222 rte_be_to_cpu_64(cq[pos + p2].timestamp)); in rxq_cq_process_v()
|
| /dpdk/examples/server_node_efd/node/ |
| H A D | node.c | 175 uint8_t p2 = info->id[i+1]; in configure_output_ports() local
177 output_ports[p1] = p2; in configure_output_ports()
178 output_ports[p2] = p1; in configure_output_ports()
181 configure_tx_buffer(p2, MBQ_CAPACITY); in configure_output_ports()
|
| /dpdk/devtools/cocci/ |
| H A D | namespace_ethdev.cocci | 38 @ script : python p2@
46 identifier p2.B;
|
| /dpdk/lib/security/ |
| H A D | rte_security.c | 20 #define RTE_PTR_CHAIN3_OR_ERR_RET(p1, p2, p3, retval, last_retval) do { \ argument
22 RTE_PTR_OR_ERR_RET(p1->p2, retval); \
23 RTE_PTR_OR_ERR_RET(p1->p2->p3, last_retval); \
|
| /dpdk/lib/hash/ |
| H A D | rte_cmp_arm64.h | 20 : [p2]"r"(key2) in rte_hash_k16_cmp_eq()
|
| /dpdk/lib/vhost/ |
| H A D | vhost.h | 647 const void *p2) in guest_page_addrcmp() argument
650 const struct guest_page *page2 = (const struct guest_page *)p2; in guest_page_addrcmp()
660 static __rte_always_inline int guest_page_rangecmp(const void *p1, const void *p2) in guest_page_rangecmp() argument
663 const struct guest_page *page2 = (const struct guest_page *)p2; in guest_page_rangecmp()
|
| /dpdk/drivers/event/sw/ |
| H A D | sw_evdev_selftest.c | 2451 const int p2 = 2; in inflight_counts() local
2470 err = rte_event_port_link(evdev, t->port[p2], &t->qid[1], NULL, 1); in inflight_counts()
2540 if (stats.port_inflight[p2] != QID2_NUM) { in inflight_counts()
2585 deq_pkts = rte_event_dequeue_burst(evdev, t->port[p2], events, in inflight_counts()
2592 if (stats.port_inflight[p2] != QID2_NUM) { in inflight_counts()
2598 err = rte_event_enqueue_burst(evdev, t->port[p2], &release_ev, in inflight_counts()
2614 if (stats.port_inflight[p2] != 0) { in inflight_counts()
|
| /dpdk/doc/guides/sample_app_ug/ |
| H A D | l2_forward_event.rst | 369 like p0--->p1, p1--->p2, p2--->p0.
426 like p0--->p1, p1--->p2, p2--->p0.
|
| /dpdk/lib/eal/linux/ |
| H A D | eal_memory.c | 498 const struct hugepage_file *p2 = b; in cmp_physaddr() local
502 const struct hugepage_file *p2 = a; 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 D | ngbe_dummy.h | 18 #define TUP2 TUP(p2)
|
| /dpdk/drivers/net/txgbe/base/ |
| H A D | txgbe_dummy.h | 18 #define TUP2 TUP(p2)
|
| /dpdk/drivers/net/cnxk/ |
| H A D | cn10k_rx.h | 1144 void *p2 = in cn10k_nix_recv_pkts_vector() local
1150 rte_prefetch0(p2); in cn10k_nix_recv_pkts_vector()
|