Home
last modified time | relevance | path

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

1234

/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 …]
/dpdk/lib/node/
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()
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()
/dpdk/lib/net/
H A Drte_net.h135 ipv4_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
151 ipv4_hdr = rte_pktmbuf_mtod_offset(m, struct rte_ipv4_hdr *, in rte_net_intel_cksum_flags_prepare()
165 ipv6_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
168 udp_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
183 ipv6_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
186 tcp_hdr = rte_pktmbuf_mtod_offset(m, in rte_net_intel_cksum_flags_prepare()
/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()
/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()
/dpdk/drivers/crypto/ipsec_mb/
H A Dpmd_snow3g.c88 return rte_pktmbuf_mtod_offset(op->sym->m_src, in snow3g_digest_appended_in_src()
114 src[i] = rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op()
120 dst[i] = rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op()
136 rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op()
139 rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op()
144 dst[i] = rte_pktmbuf_mtod_offset(ops[i]->sym->m_src, in process_snow3g_cipher_op()
208 rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op_bit()
211 rte_pktmbuf_mtod_offset( in process_snow3g_cipher_op_bit()
264 src = rte_pktmbuf_mtod_offset( in process_snow3g_hash_op()
/dpdk/lib/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()
/dpdk/drivers/compress/isal/
H A Disal_compress_pmd.c253 qp->stream->next_in = rte_pktmbuf_mtod_offset(src, uint8_t *, in chained_mbuf_compression()
262 qp->stream->next_out = rte_pktmbuf_mtod_offset(dst, uint8_t *, in chained_mbuf_compression()
343 qp->state->next_in = rte_pktmbuf_mtod_offset(src, uint8_t *, in chained_mbuf_decompression()
352 qp->state->next_out = rte_pktmbuf_mtod_offset(dst, uint8_t *, in chained_mbuf_decompression()
476 qp->stream->next_in = rte_pktmbuf_mtod_offset(op->m_src, in process_isal_deflate()
481 qp->stream->next_out = rte_pktmbuf_mtod_offset(op->m_dst, in process_isal_deflate()
567 qp->state->next_in = rte_pktmbuf_mtod_offset(op->m_src, in process_isal_inflate()
572 qp->state->next_out = rte_pktmbuf_mtod_offset(op->m_dst, in process_isal_inflate()
/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()
/dpdk/lib/ipsec/
H A Desp_inb.c72 ivp = rte_pktmbuf_mtod_offset(mb, uint64_t *, in inb_cop_prepare()
146 ivp = rte_pktmbuf_mtod_offset(mb, uint64_t *, in inb_cpu_crypto_prepare()
196 prev = rte_pktmbuf_mtod_offset(ml, const void *, ofs); in move_icv()
260 esph = rte_pktmbuf_mtod_offset(mb, struct rte_esp_hdr *, hlen); in inb_get_sqn()
326 icv->va = rte_pktmbuf_mtod_offset(ml, void *, icv_ofs); in inb_prepare()
422 pt = rte_pktmbuf_mtod_offset(ml[0], const struct rte_esp_tail *, ofs); in process_step1()
440 pd = rte_pktmbuf_mtod_offset(mb, const uint8_t *, ofs); in check_pad_bytes()
503 ph = rte_pktmbuf_mtod_offset(mb, const struct rte_esp_hdr *, hlen); in tun_process_step2()
610 outh = rte_pktmbuf_mtod_offset(mb[i], uint8_t *, in tun_process()
/dpdk/app/test-pmd/
H A Dtxonly.c82 seg_buf = rte_pktmbuf_mtod_offset(seg, char *, offset); in copy_buf_to_pkt_segs()
98 rte_memcpy(rte_pktmbuf_mtod_offset(pkt, char *, offset), in copy_buf_to_pkt()
174 udp_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_udp_hdr *, in update_pkt_header()
181 ip_hdr = rte_pktmbuf_mtod_offset(pkt, struct rte_ipv4_hdr *, in update_pkt_header()
239 ip_hdr = rte_pktmbuf_mtod_offset(pkt, in pkt_burst_prepare()
H A Dutil.c249 ipv4_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
255 ipv6_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
261 udp_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
265 vxlan_hdr = rte_pktmbuf_mtod_offset(mb, in dump_pkt_burst()
/dpdk/drivers/crypto/qat/
H A Dqat_sym.h181 last_block = (uint8_t *) rte_pktmbuf_mtod_offset(sym_op->m_src, in qat_bpicipher_postprocess()
186 dst = (uint8_t *) rte_pktmbuf_mtod_offset(sym_op->m_dst, in qat_bpicipher_postprocess()
234 crc_data = rte_pktmbuf_mtod_offset(sym_op->m_src, uint8_t *, in qat_crc_verify()
258 crc_data = rte_pktmbuf_mtod_offset(sym_op->m_src, uint8_t *, in qat_crc_generate()
/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()
/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()
/dpdk/app/test/
H A Dtest_cksum.c116 l3_hdr = rte_pktmbuf_mtod_offset(m, void *, hdr_lens.l2_len); in test_l4_cksum()
117 l4_hdr = rte_pktmbuf_mtod_offset(m, void *, in test_l4_cksum()
H A Dtest_cryptodev.h126 dst = rte_pktmbuf_mtod_offset(m, char *, offset); in pktmbuf_write()
160 return rte_pktmbuf_mtod_offset(m, uint8_t *, offset); in pktmbuf_mtod_offset()
/dpdk/drivers/baseband/turbo_sw/
H A Dbbdev_turbo_software.c580 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_enc_cb()
692 out0 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_enc_cb()
693 out1 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, in process_enc_cb()
695 out2 = rte_pktmbuf_mtod_offset(m_out, uint8_t *, in process_enc_cb()
868 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_ldpc_enc_cb()
1250 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_dec_cb()
1309 out = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_dec_cb()
1400 in = rte_pktmbuf_mtod_offset(m_in, uint8_t *, in_offset); in process_ldpc_dec_cb()
1409 harq_in = rte_pktmbuf_mtod_offset(m_harq_in, in process_ldpc_dec_cb()
1466 out = rte_pktmbuf_mtod_offset(m_out, uint8_t *, out_offset); in process_ldpc_dec_cb()
[all …]
/dpdk/lib/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()
/dpdk/lib/mbuf/
H A Drte_mbuf.c564 buffer = rte_pktmbuf_mtod_offset(mbuf, char *, mbuf->data_len); in __rte_pktmbuf_linearize()
646 rte_memcpy(rte_pktmbuf_mtod_offset(m_last, char *, in rte_pktmbuf_copy()
648 rte_pktmbuf_mtod_offset(seg, char *, off), in rte_pktmbuf_copy()
718 return rte_pktmbuf_mtod_offset(seg, char *, off); in __rte_pktmbuf_read()
726 rte_pktmbuf_mtod_offset(seg, char *, off), copy_len); in __rte_pktmbuf_read()

1234