| /f-stack/dpdk/drivers/net/octeontx2/ |
| H A D | otx2_tx.c | 161 mbuf1 = (uint64_t *)tx_pkts[1]; in nix_xmit_pkts_vector()
167 mbuf1 = (uint64_t *)((uintptr_t)mbuf1 + in nix_xmit_pkts_vector()
182 dataoff_iova1 = vld1q_u64(mbuf1); in nix_xmit_pkts_vector()
183 len_olflags1 = vld1q_u64(mbuf1 + 2); in nix_xmit_pkts_vector()
268 mbuf1 = (uint64_t *)((uintptr_t)mbuf1 + in nix_xmit_pkts_vector()
305 mbuf1 = (uint64_t *)*mbuf1; in nix_xmit_pkts_vector()
311 mbuf1 = (uint64_t *)*mbuf1; in nix_xmit_pkts_vector()
424 mbuf1 = (uint64_t *)((uintptr_t)mbuf1 + in nix_xmit_pkts_vector()
581 mbuf1 = (uint64_t *)((uintptr_t)mbuf1 + in nix_xmit_pkts_vector()
813 mbuf1 = (uint64_t *)((uintptr_t)mbuf1 + in nix_xmit_pkts_vector()
[all …]
|
| H A D | otx2_rx.c | 126 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3; in nix_recv_pkts_vector() local
171 mbuf1 = (struct rte_mbuf *)vgetq_lane_u64(mbuf01, 1); in nix_recv_pkts_vector()
248 ol_flags1 = nix_qinq_update(cq1_w2, ol_flags1, mbuf1); in nix_recv_pkts_vector()
257 (cq0 + CQE_SZ(1) + 38), ol_flags1, mbuf1); in nix_recv_pkts_vector()
272 vst1q_u64((uint64_t *)mbuf1->rx_descriptor_fields1, f1); in nix_recv_pkts_vector()
278 vst1q_u64((uint64_t *)mbuf1->rearm_data, rearm1); in nix_recv_pkts_vector()
288 otx2_prefetch_store_keep(mbuf1); in nix_recv_pkts_vector()
294 __mempool_check_cookies(mbuf1->pool, (void **)&mbuf1, 1, 1); in nix_recv_pkts_vector()
|
| /f-stack/dpdk/lib/librte_node/ |
| H A D | ip4_lookup_sse.h | 13 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3, **pkts; in ip4_lookup_node_process_vec() local
67 mbuf1 = pkts[1]; in ip4_lookup_node_process_vec()
83 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf1, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
87 node_mbuf_priv1(mbuf1, dyn)->cksum = ipv4_hdr->hdr_checksum; in ip4_lookup_node_process_vec()
88 node_mbuf_priv1(mbuf1, dyn)->ttl = ipv4_hdr->time_to_live; in ip4_lookup_node_process_vec()
122 node_mbuf_priv1(mbuf1, dyn)->nh = dst.u32[1] & 0xFFFF; in ip4_lookup_node_process_vec()
|
| H A D | ethdev_rx.c | 71 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3; in eth_pkt_parse_cb() local
102 mbuf1 = pkts[1]; in eth_pkt_parse_cb()
114 eth_hdr = rte_pktmbuf_mtod(mbuf1, struct rte_ether_hdr *); in eth_pkt_parse_cb()
116 mbuf1->packet_type = l3_ptype(etype, 0); in eth_pkt_parse_cb()
|
| H A D | ip4_lookup_neon.h | 13 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3, **pkts; in ip4_lookup_node_process_vec() local
71 mbuf1 = pkts[1]; in ip4_lookup_node_process_vec()
87 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf1, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
121 node_mbuf_priv1(mbuf1, dyn)->u = priv01.u64[1]; in ip4_lookup_node_process_vec()
|
| H A D | pkt_cls.c | 37 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3, **pkts; in pkt_cls_node_process() local
75 mbuf1 = pkts[1]; in pkt_cls_node_process()
83 l1 = mbuf1->packet_type & in pkt_cls_node_process()
|
| H A D | ip4_rewrite.c | 41 struct rte_mbuf *mbuf0, *mbuf1, *mbuf2, *mbuf3, **pkts; in ip4_rewrite_node_process() local
79 mbuf1 = pkts[1]; in ip4_rewrite_node_process()
86 priv01.u64[1] = node_mbuf_priv1(mbuf1, dyn)->u; in ip4_rewrite_node_process()
108 d1 = rte_pktmbuf_mtod(mbuf1, void *); in ip4_rewrite_node_process()
|
| /f-stack/dpdk/lib/librte_pipeline/ |
| H A D | rte_table_action.c | 2093 struct rte_mbuf *mbuf1, in pkt4_work_tag() argument
2102 mbuf1->hash.fdir.hi = data1->tag; in pkt4_work_tag()
2143 struct rte_mbuf *mbuf1, in pkt4_work_decap() argument
2176 mbuf1->data_off = data_off1 + n1; in pkt4_work_decap()
2177 mbuf1->data_len = data_len1 - n1; in pkt4_work_decap()
2178 mbuf1->pkt_len = pkt_len1 - n1; in pkt4_work_decap()
3025 struct rte_mbuf *mbuf1 = mbufs[1]; in pkt4_work() local
3093 pkt_work_lb(mbuf1, in pkt4_work()
3124 drop_mask1 |= pkt_work_mtr(mbuf1, in pkt4_work()
3164 pkt_work_tm(mbuf1, in pkt4_work()
[all …]
|
| /f-stack/dpdk/lib/librte_table/ |
| H A D | rte_table_hash_key16.c | 649 #define lookup1_stage1(mbuf1, bucket1, f) \ argument
655 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf1, f->key_offset);\
|
| H A D | rte_table_hash_key8.c | 621 #define lookup1_stage1(mbuf1, bucket1, f) \ argument
627 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf1, f->key_offset);\
|
| H A D | rte_table_hash_key32.c | 677 #define lookup1_stage1(mbuf1, bucket1, f) \ argument
683 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf1, f->key_offset); \
|
| /f-stack/dpdk/doc/guides/prog_guide/ |
| H A D | mbuf_lib.rst | 50 .. figure:: img/mbuf1.*
|
| /f-stack/dpdk/doc/guides/contributing/ |
| H A D | documentation.rst | 462 …Use some of the older images in ``doc/guides/prog_guide/img/`` as a template, for example ``mbuf1.…
|