| /f-stack/dpdk/drivers/net/octeontx2/ |
| H A D | otx2_tx.c | 162 mbuf2 = (uint64_t *)tx_pkts[2]; in nix_xmit_pkts_vector()
169 mbuf2 = (uint64_t *)((uintptr_t)mbuf2 + in nix_xmit_pkts_vector()
184 dataoff_iova2 = vld1q_u64(mbuf2); in nix_xmit_pkts_vector()
185 len_olflags2 = vld1q_u64(mbuf2 + 2); in nix_xmit_pkts_vector()
271 mbuf2 = (uint64_t *)((uintptr_t)mbuf2 + in nix_xmit_pkts_vector()
306 mbuf2 = (uint64_t *)*mbuf2; in nix_xmit_pkts_vector()
312 mbuf2 = (uint64_t *)*mbuf2; in nix_xmit_pkts_vector()
426 mbuf2 = (uint64_t *)((uintptr_t)mbuf2 + in nix_xmit_pkts_vector()
583 mbuf2 = (uint64_t *)((uintptr_t)mbuf2 + in nix_xmit_pkts_vector()
815 mbuf2 = (uint64_t *)((uintptr_t)mbuf2 + 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
172 mbuf2 = (struct rte_mbuf *)vgetq_lane_u64(mbuf23, 0); in nix_recv_pkts_vector()
249 ol_flags2 = nix_qinq_update(cq2_w2, ol_flags2, mbuf2); in nix_recv_pkts_vector()
259 (cq0 + CQE_SZ(2) + 38), ol_flags2, mbuf2); in nix_recv_pkts_vector()
273 vst1q_u64((uint64_t *)mbuf2->rx_descriptor_fields1, f2); in nix_recv_pkts_vector()
279 vst1q_u64((uint64_t *)mbuf2->rearm_data, rearm2); in nix_recv_pkts_vector()
289 otx2_prefetch_store_keep(mbuf2); in nix_recv_pkts_vector()
295 __mempool_check_cookies(mbuf2->pool, (void **)&mbuf2, 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
68 mbuf2 = pkts[2]; in ip4_lookup_node_process_vec()
91 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf2, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
95 node_mbuf_priv1(mbuf2, dyn)->cksum = ipv4_hdr->hdr_checksum; in ip4_lookup_node_process_vec()
96 node_mbuf_priv1(mbuf2, dyn)->ttl = ipv4_hdr->time_to_live; in ip4_lookup_node_process_vec()
125 node_mbuf_priv1(mbuf2, dyn)->nh = dst.u32[2] & 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
103 mbuf2 = pkts[2]; in eth_pkt_parse_cb()
119 eth_hdr = rte_pktmbuf_mtod(mbuf2, struct rte_ether_hdr *); in eth_pkt_parse_cb()
121 mbuf2->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
72 mbuf2 = pkts[2]; in ip4_lookup_node_process_vec()
95 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf2, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
122 node_mbuf_priv1(mbuf2, dyn)->u = priv23.u64[0]; 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
76 mbuf2 = pkts[2]; in pkt_cls_node_process()
85 l2 = mbuf2->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
80 mbuf2 = pkts[2]; in ip4_rewrite_node_process()
87 priv23.u64[0] = node_mbuf_priv1(mbuf2, dyn)->u; in ip4_rewrite_node_process()
119 d2 = rte_pktmbuf_mtod(mbuf2, void *); in ip4_rewrite_node_process()
|
| /f-stack/dpdk/lib/librte_pipeline/ |
| H A D | rte_table_action.c | 2094 struct rte_mbuf *mbuf2, in pkt4_work_tag() argument
2103 mbuf2->hash.fdir.hi = data2->tag; in pkt4_work_tag()
2144 struct rte_mbuf *mbuf2, in pkt4_work_decap() argument
2180 mbuf2->data_off = data_off2 + n2; in pkt4_work_decap()
2181 mbuf2->data_len = data_len2 - n2; in pkt4_work_decap()
2182 mbuf2->pkt_len = pkt_len2 - n2; in pkt4_work_decap()
3026 struct rte_mbuf *mbuf2 = mbufs[2]; in pkt4_work() local
3097 pkt_work_lb(mbuf2, in pkt4_work()
3132 drop_mask2 |= pkt_work_mtr(mbuf2, in pkt4_work()
3169 pkt_work_tm(mbuf2, in pkt4_work()
[all …]
|
| /f-stack/dpdk/lib/librte_table/ |
| H A D | rte_table_hash_key16.c | 665 #define lookup1_stage2_lru(pkt2_index, mbuf2, bucket2, \ argument
673 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
685 #define lookup1_stage2_ext(pkt2_index, mbuf2, bucket2, pkts_mask_out, entries, \ argument
694 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
|
| H A D | rte_table_hash_key8.c | 635 #define lookup1_stage2_lru(pkt2_index, mbuf2, bucket2, \ argument
643 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
655 #define lookup1_stage2_ext(pkt2_index, mbuf2, bucket2, pkts_mask_out,\ argument
664 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
|
| H A D | rte_table_hash_key32.c | 694 #define lookup1_stage2_lru(pkt2_index, mbuf2, bucket2, \ argument
702 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
714 #define lookup1_stage2_ext(pkt2_index, mbuf2, bucket2, pkts_mask_out,\ argument
723 key = RTE_MBUF_METADATA_UINT64_PTR(mbuf2, f->key_offset);\
|
| /f-stack/dpdk/doc/guides/prog_guide/ |
| H A D | mbuf_lib.rst | 57 .. figure:: img/mbuf2.*
|