Home
last modified time | relevance | path

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

1234

/f-stack/dpdk/devtools/cocci/
H A Dmtod-offset.cocci10 + rte_pktmbuf_mtod_offset(M, char *, O)
13 + rte_pktmbuf_mtod_offset(M, char *, -O)
22 + rte_pktmbuf_mtod_offset(M, uint8_t *, O)
25 + rte_pktmbuf_mtod_offset(M, uint8_t *, -O)
31 // rte_pktmbuf_mtod_offset().
37 - rte_pktmbuf_mtod_offset(M, char *, O1) + O2
38 + rte_pktmbuf_mtod_offset(M, char *, O1 + O2)
65 - (C)rte_pktmbuf_mtod_offset(M, T, O)
66 + rte_pktmbuf_mtod_offset(M, C, O)
68 - (rte_pktmbuf_mtod_offset(M, T, O))
[all …]
/f-stack/dpdk/lib/librte_node/
H A Dip4_lookup_sse.h39 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[i], void *, in ip4_lookup_node_process_vec()
56 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[4], void *, in ip4_lookup_node_process_vec()
58 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[5], void *, in ip4_lookup_node_process_vec()
60 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[6], void *, in ip4_lookup_node_process_vec()
62 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[7], void *, in ip4_lookup_node_process_vec()
75 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf0, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
83 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf1, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
91 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf2, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
99 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf3, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
200 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf0, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
H A Dip4_lookup_neon.h42 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[i], void *, in ip4_lookup_node_process_vec()
60 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[4], void *, in ip4_lookup_node_process_vec()
62 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[5], void *, in ip4_lookup_node_process_vec()
64 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[6], void *, in ip4_lookup_node_process_vec()
66 rte_prefetch0(rte_pktmbuf_mtod_offset(pkts[7], void *, in ip4_lookup_node_process_vec()
79 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf0, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
87 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf1, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
95 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf2, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
103 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf3, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
195 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf0, struct rte_ipv4_hdr *, in ip4_lookup_node_process_vec()
/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_em_hlm_neon.h15 int32x4_t tmpdata0 = vld1q_s32(rte_pktmbuf_mtod_offset(m0, int32_t *, in get_ipv4_5tuple()
27 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
32 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
37 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
H A Dl3fwd_em_hlm_sse.h15 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv4_5tuple()
27 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
32 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
38 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
H A Dl3fwd_lpm.h20 ipv4_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv4_hdr *, in l3fwd_lpm_simple_forward()
54 ipv6_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv6_hdr *, in l3fwd_lpm_simple_forward()
H A Dl3fwd_em_sequential.h39 ipv4_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_ipv4_hdr *, in em_get_dst_port()
54 ipv6_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_ipv6_hdr *, in em_get_dst_port()
H A Dl3fwd_em.h16 ipv4_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv4_hdr *, in l3fwd_em_handle_ipv4()
56 ipv6_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv6_hdr *, in l3fwd_em_handle_ipv6()
/f-stack/dpdk/lib/librte_net/
H A Drte_net.h144 ipv4_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv4_hdr *, in rte_net_intel_cksum_flags_prepare()
158 ipv6_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
161 udp_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
176 ipv6_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
179 tcp_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
/f-stack/dpdk/drivers/crypto/bcmfs/
H A Dbcmfs_sym.c34 fsattr_va(&src) = rte_pktmbuf_mtod_offset in process_crypto_cipher_op()
39 fsattr_va(&dst) = rte_pktmbuf_mtod_offset in process_crypto_cipher_op()
77 fsattr_va(&src) = rte_pktmbuf_mtod_offset(mbuf_src, in process_crypto_auth_op()
137 fsattr_va(&src) = rte_pktmbuf_mtod_offset in process_crypto_combined_op()
142 fsattr_va(&dst) = rte_pktmbuf_mtod_offset in process_crypto_combined_op()
175 fsattr_va(&aad) = rte_pktmbuf_mtod_offset in process_crypto_combined_op()
214 fsattr_va(&src) = rte_pktmbuf_mtod_offset(mbuf_src, in process_crypto_aead_op()
218 fsattr_va(&dst) = rte_pktmbuf_mtod_offset(mbuf_dst, in process_crypto_aead_op()
/f-stack/dpdk/drivers/crypto/qat/
H A Dqat_sym.h98 last_block = (uint8_t *) rte_pktmbuf_mtod_offset(sym_op->m_src, in qat_bpicipher_postprocess()
103 dst = (uint8_t *) rte_pktmbuf_mtod_offset(sym_op->m_dst, in qat_bpicipher_postprocess()
151 crc_data = rte_pktmbuf_mtod_offset(sym_op->m_src, uint8_t *, in qat_crc_verify()
175 crc_data = rte_pktmbuf_mtod_offset(sym_op->m_src, uint8_t *, in qat_crc_generate()
/f-stack/dpdk/lib/librte_gso/
H A Dgso_udp4.c25 ipv4_hdr = rte_pktmbuf_mtod_offset(segs[i], in update_ipv4_udp_headers()
51 ipv4_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_ipv4_hdr *, in gso_udp4_segment()
/f-stack/dpdk/lib/librte_ipsec/
H A Desp_inb.c71 ivp = rte_pktmbuf_mtod_offset(mb, uint64_t *, in inb_cop_prepare()
117 ivp = rte_pktmbuf_mtod_offset(mb, uint64_t *, in inb_cpu_crypto_prepare()
157 prev = rte_pktmbuf_mtod_offset(ml, const void *, ofs); in move_icv()
201 esph = rte_pktmbuf_mtod_offset(mb, struct rte_esp_hdr *, hlen); in inb_get_sqn()
267 icv->va = rte_pktmbuf_mtod_offset(ml, void *, icv_ofs); in inb_prepare()
363 pt = rte_pktmbuf_mtod_offset(ml[0], const struct rte_esp_tail *, ofs); in process_step1()
381 pd = rte_pktmbuf_mtod_offset(mb, const uint8_t *, ofs); in check_pad_bytes()
444 ph = rte_pktmbuf_mtod_offset(mb, const struct rte_esp_hdr *, hlen); in tun_process_step2()
550 outh = rte_pktmbuf_mtod_offset(mb[i], uint8_t *, in tun_process()
/f-stack/dpdk/drivers/compress/isal/
H A Disal_compress_pmd.c249 qp->stream->next_in = rte_pktmbuf_mtod_offset(src, uint8_t *, in chained_mbuf_compression()
258 qp->stream->next_out = rte_pktmbuf_mtod_offset(dst, uint8_t *, in chained_mbuf_compression()
339 qp->state->next_in = rte_pktmbuf_mtod_offset(src, uint8_t *, in chained_mbuf_decompression()
348 qp->state->next_out = rte_pktmbuf_mtod_offset(dst, uint8_t *, in chained_mbuf_decompression()
472 qp->stream->next_in = rte_pktmbuf_mtod_offset(op->m_src, in process_isal_deflate()
477 qp->stream->next_out = rte_pktmbuf_mtod_offset(op->m_dst, in process_isal_deflate()
563 qp->state->next_in = rte_pktmbuf_mtod_offset(op->m_src, in process_isal_inflate()
568 qp->state->next_out = rte_pktmbuf_mtod_offset(op->m_dst, in process_isal_inflate()
/f-stack/dpdk/drivers/compress/zlib/
H A Dzlib_pmd.c42 strm->next_in = rte_pktmbuf_mtod_offset(mbuf_src, uint8_t *, in process_zlib_deflate()
47 strm->next_out = rte_pktmbuf_mtod_offset(mbuf_dst, uint8_t *, in process_zlib_deflate()
120 strm->next_in = rte_pktmbuf_mtod_offset(mbuf_src, uint8_t *, in process_zlib_inflate()
125 strm->next_out = rte_pktmbuf_mtod_offset(mbuf_dst, uint8_t *, in process_zlib_inflate()
/f-stack/dpdk/app/test-pmd/
H A Dtxonly.c80 seg_buf = rte_pktmbuf_mtod_offset(seg, char *, offset); in copy_buf_to_pkt_segs()
96 rte_memcpy(rte_pktmbuf_mtod_offset(pkt, char *, offset), in copy_buf_to_pkt()
172 udp_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_udp_hdr *, in update_pkt_header()
179 ip_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_ipv4_hdr *, in update_pkt_header()
237 ip_hdr = rte_pktmbuf_mtod_offset(pkt, in pkt_burst_prepare()
H A Dutil.c200 ipv4_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
206 ipv6_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
212 udp_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
216 vxlan_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c912 ipv4_hdr[0] = rte_pktmbuf_mtod_offset(m[0], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
914 ipv4_hdr[1] = rte_pktmbuf_mtod_offset(m[1], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
916 ipv4_hdr[2] = rte_pktmbuf_mtod_offset(m[2], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
918 ipv4_hdr[3] = rte_pktmbuf_mtod_offset(m[3], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
920 ipv4_hdr[4] = rte_pktmbuf_mtod_offset(m[4], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
922 ipv4_hdr[5] = rte_pktmbuf_mtod_offset(m[5], struct rte_ipv4_hdr *, in simple_ipv4_fwd_8pkts()
1104 __m128i tmpdata0 = _mm_loadu_si128(rte_pktmbuf_mtod_offset(m0, in get_ipv6_5tuple()
1107 __m128i tmpdata1 = _mm_loadu_si128(rte_pktmbuf_mtod_offset(m0, in get_ipv6_5tuple()
1111 __m128i tmpdata2 = _mm_loadu_si128(rte_pktmbuf_mtod_offset(m0, in get_ipv6_5tuple()
1248 ipv4_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv4_hdr *, in l3fwd_simple_forward()
[all …]
/f-stack/dpdk/examples/ipsec-secgw/
H A Desp.c85 sym_cop->aead.digest.data = rte_pktmbuf_mtod_offset(m, void*, in esp_inbound()
134 sym_cop->auth.digest.data = rte_pktmbuf_mtod_offset(m, void*, in esp_inbound()
180 nexthdr = rte_pktmbuf_mtod_offset(m, uint8_t*, in esp_inbound_post()
395 sym_cop->aead.digest.data = rte_pktmbuf_mtod_offset(m, uint8_t *, in esp_outbound()
444 sym_cop->auth.digest.data = rte_pktmbuf_mtod_offset(m, uint8_t *, in esp_outbound()
/f-stack/dpdk/app/test/
H A Dtest_cryptodev.h108 dst = rte_pktmbuf_mtod_offset(m, char *, offset); in pktmbuf_write()
142 return rte_pktmbuf_mtod_offset(m, uint8_t *, offset); in pktmbuf_mtod_offset()
/f-stack/dpdk/lib/librte_mbuf/
H A Drte_mbuf_core.h711 #define rte_pktmbuf_mtod_offset(m, t, o) \ macro
726 #define rte_pktmbuf_mtod(m, t) rte_pktmbuf_mtod_offset(m, t, 0)
H A Drte_mbuf.c570 buffer = rte_pktmbuf_mtod_offset(mbuf, char *, mbuf->data_len); in __rte_pktmbuf_linearize()
652 rte_memcpy(rte_pktmbuf_mtod_offset(m_last, char *, in rte_pktmbuf_copy()
654 rte_pktmbuf_mtod_offset(seg, char *, off), in rte_pktmbuf_copy()
724 return rte_pktmbuf_mtod_offset(seg, char *, off); in __rte_pktmbuf_read()
732 rte_pktmbuf_mtod_offset(seg, char *, off), copy_len); in __rte_pktmbuf_read()
/f-stack/dpdk/drivers/net/hinic/
H A Dhinic_pmd_tx.c798 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv4_hdr *, in hinic_analyze_tx_info()
825 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv4_hdr *, in hinic_analyze_outer_ip_vxlan()
836 udp_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_udp_hdr *, in hinic_analyze_outer_ip_vxlan()
870 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv4_hdr *, in hinic_calculate_tcp_checksum()
880 ipv6_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv6_hdr *, in hinic_calculate_tcp_checksum()
882 tcp_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_tcp_hdr *, in hinic_calculate_tcp_checksum()
902 ipv4_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv4_hdr *, in hinic_calculate_udp_checksum()
913 ipv6_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_ipv6_hdr *, in hinic_calculate_udp_checksum()
916 udp_hdr = rte_pktmbuf_mtod_offset(mbuf, struct rte_udp_hdr *, in hinic_calculate_udp_checksum()
/f-stack/dpdk/lib/librte_ip_frag/
H A Drte_ipv6_reassembly.c93 ip_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv6_hdr *, m->l2_len); in ipv6_frag_reassemble()
108 ip_frag_memmove(rte_pktmbuf_mtod_offset(m, char *, sizeof(*frag_hdr)), in ipv6_frag_reassemble()
/f-stack/dpdk/drivers/baseband/turbo_sw/
H A Dbbdev_turbo_software.c577 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_enc_cb()
689 out0 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_enc_cb()
690 out1 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, in process_enc_cb()
692 out2 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, in process_enc_cb()
865 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_ldpc_enc_cb()
1241 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_dec_cb()
1300 out = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_dec_cb()
1391 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_ldpc_dec_cb()
1400 harq_in = rte_pktmbuf_mtod_offset(m_harq_in, in process_ldpc_dec_cb()
1457 out = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_ldpc_dec_cb()
[all …]

1234