| /f-stack/dpdk/drivers/net/octeontx2/ |
| H A D | otx2_tx.c | 163 mbuf3 = (uint64_t *)tx_pkts[3]; in nix_xmit_pkts_vector()
171 mbuf3 = (uint64_t *)((uintptr_t)mbuf3 + in nix_xmit_pkts_vector()
186 dataoff_iova3 = vld1q_u64(mbuf3); in nix_xmit_pkts_vector()
187 len_olflags3 = vld1q_u64(mbuf3 + 2); in nix_xmit_pkts_vector()
274 mbuf3 = (uint64_t *)((uintptr_t)mbuf3 + in nix_xmit_pkts_vector()
307 mbuf3 = (uint64_t *)*mbuf3; in nix_xmit_pkts_vector()
313 mbuf3 = (uint64_t *)*mbuf3; in nix_xmit_pkts_vector()
428 mbuf3 = (uint64_t *)((uintptr_t)mbuf3 + in nix_xmit_pkts_vector()
585 mbuf3 = (uint64_t *)((uintptr_t)mbuf3 + in nix_xmit_pkts_vector()
817 mbuf3 = (uint64_t *)((uintptr_t)mbuf3 + 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
173 mbuf3 = (struct rte_mbuf *)vgetq_lane_u64(mbuf23, 1); in nix_recv_pkts_vector()
250 ol_flags3 = nix_qinq_update(cq3_w2, ol_flags3, mbuf3); in nix_recv_pkts_vector()
261 (cq0 + CQE_SZ(3) + 38), ol_flags3, mbuf3); in nix_recv_pkts_vector()
274 vst1q_u64((uint64_t *)mbuf3->rx_descriptor_fields1, f3); in nix_recv_pkts_vector()
280 vst1q_u64((uint64_t *)mbuf3->rearm_data, rearm3); in nix_recv_pkts_vector()
290 otx2_prefetch_store_keep(mbuf3); in nix_recv_pkts_vector()
296 __mempool_check_cookies(mbuf3->pool, (void **)&mbuf3, 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
69 mbuf3 = pkts[3]; in ip4_lookup_node_process_vec()
99 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf3, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
112 node_mbuf_priv1(mbuf3, dyn)->cksum = ipv4_hdr->hdr_checksum; in ip4_lookup_node_process_vec()
113 node_mbuf_priv1(mbuf3, dyn)->ttl = ipv4_hdr->time_to_live; in ip4_lookup_node_process_vec()
128 node_mbuf_priv1(mbuf3, dyn)->nh = dst.u32[3] & 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
104 mbuf3 = pkts[3]; in eth_pkt_parse_cb()
124 eth_hdr = rte_pktmbuf_mtod(mbuf3, struct rte_ether_hdr *); in eth_pkt_parse_cb()
126 mbuf3->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
73 mbuf3 = pkts[3]; in ip4_lookup_node_process_vec()
103 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf3, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
123 node_mbuf_priv1(mbuf3, dyn)->u = priv23.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
77 mbuf3 = pkts[3]; in pkt_cls_node_process()
87 l3 = mbuf3->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
81 mbuf3 = pkts[3]; in ip4_rewrite_node_process()
88 priv23.u64[1] = node_mbuf_priv1(mbuf3, dyn)->u; in ip4_rewrite_node_process()
129 d3 = rte_pktmbuf_mtod(mbuf3, void *); in ip4_rewrite_node_process()
|
| /f-stack/dpdk/lib/librte_pipeline/ |
| H A D | rte_table_action.c | 2095 struct rte_mbuf *mbuf3, in pkt4_work_tag() argument
2104 mbuf3->hash.fdir.hi = data3->tag; in pkt4_work_tag()
2145 struct rte_mbuf *mbuf3, in pkt4_work_decap() argument
2184 mbuf3->data_off = data_off3 + n3; in pkt4_work_decap()
2185 mbuf3->data_len = data_len3 - n3; in pkt4_work_decap()
2186 mbuf3->pkt_len = pkt_len3 - n3; in pkt4_work_decap()
3027 struct rte_mbuf *mbuf3 = mbufs[3]; in pkt4_work() local
3101 pkt_work_lb(mbuf3, in pkt4_work()
3140 drop_mask3 |= pkt_work_mtr(mbuf3, in pkt4_work()
3174 pkt_work_tm(mbuf3, in pkt4_work()
[all …]
|