| /dpdk/examples/l3fwd/ |
| H A D | l3fwd_lpm_neon.h | 18 int32x4_t *dip, in processx4_step1() argument
45 dip[0] = vld1q_s32(dst); in processx4_step1()
54 int32x4_t dip, in processx4_step2() argument
62 dip = vreinterpretq_s32_u8(vrev32q_u8(vreinterpretq_u8_s32(dip))); in processx4_step2()
66 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, dip, dst.u32, in processx4_step2()
71 dst.x = dip; in processx4_step2()
93 int32x4_t dip; in l3fwd_lpm_send_packets() local
111 processx4_step1(&pkts_burst[j], &dip, &ipv4_flag); in l3fwd_lpm_send_packets()
112 processx4_step2(qconf, dip, ipv4_flag, portid, in l3fwd_lpm_send_packets()
116 processx4_step1(&pkts_burst[j], &dip, &ipv4_flag); in l3fwd_lpm_send_packets()
[all …]
|
| H A D | l3fwd_lpm_sse.h | 15 __m128i *dip, in processx4_step1() argument
42 dip[0] = _mm_set_epi32(x3, x2, x1, x0); in processx4_step1()
51 __m128i dip, in processx4_step2() argument
62 dip = _mm_shuffle_epi8(dip, bswap_mask); in processx4_step2()
66 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, dip, dst.u32, in processx4_step2()
72 dst.x = dip; in processx4_step2()
90 __m128i dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets() local
95 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
99 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
|
| H A D | l3fwd_lpm_altivec.h | 17 __vector unsigned int *dip, in processx4_step1() argument
48 dip[0] = (__vector unsigned int){x0, x1, x2, x3}; in processx4_step1()
57 __vector unsigned int dip, in processx4_step2() argument
71 dip = (__vector unsigned int)vec_perm(*(__vector unsigned char *)&dip, in processx4_step2()
76 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, (xmm_t)dip, in processx4_step2()
82 dst.x = (xmm_t)dip; in processx4_step2()
104 __vector unsigned int dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets() local
109 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
113 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
|
| /dpdk/lib/node/ |
| H A D | ip4_lookup_neon.h | 26 int32x4_t dip; in ip4_lookup_node_process_vec() local
45 dip = vdupq_n_s32(0); in ip4_lookup_node_process_vec()
81 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 0); in ip4_lookup_node_process_vec()
89 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 1); in ip4_lookup_node_process_vec()
97 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 2); in ip4_lookup_node_process_vec()
105 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 3); in ip4_lookup_node_process_vec()
107 dip = vreinterpretq_s32_u8( in ip4_lookup_node_process_vec()
108 vrev32q_u8(vreinterpretq_u8_s32(dip))); in ip4_lookup_node_process_vec()
114 rte_lpm_lookupx4(lpm, dip, result.u32, drop_nh); in ip4_lookup_node_process_vec()
|
| H A D | ip4_lookup_sse.h | 25 __m128i dip; /* SSE register */ in ip4_lookup_node_process_vec() local
104 dip = _mm_set_epi32(ip3, ip2, ip1, ip0); in ip4_lookup_node_process_vec()
109 dip = _mm_shuffle_epi8(dip, bswap_mask); in ip4_lookup_node_process_vec()
116 rte_lpm_lookupx4(lpm, dip, dst.u32, drop_nh); in ip4_lookup_node_process_vec()
|
| /dpdk/app/test-sad/ |
| H A D | main.c | 192 &tbl[j].tuple.v6.dip); in parse_file()
195 &tbl[j].tuple.v4.dip); in parse_file()
276 tbl[i].tuple.v6.dip[j] = in get_random_rules()
291 memcpy(tbl[i].tuple.v6.dip, in get_random_rules()
450 print_addr(af, dip); in print_tuple()
466 const void *dip, *sip; in print_result() local
474 dip = (config.ipv6 == 0) ? &v4->dip : (const void *)v6->dip; in print_result()
479 print_tuple(af, spi, dip, sip); in print_result()
498 print_tuple(af, spi, dip, sip); in print_result()
502 dip = (config.ipv6 == 0) ? &v4->dip : (const void *)v6->dip; in print_result()
[all …]
|
| /dpdk/lib/ipsec/ |
| H A D | rte_ipsec_sad.h | 36 uint32_t dip; member
42 uint8_t dip[16]; member
|
| H A D | ipsec_sad.c | 321 sizeof(((struct rte_ipsec_sadv6_key *)0)->dip); in rte_ipsec_sad_create()
324 sizeof(((struct rte_ipsec_sadv4_key *)0)->dip); in rte_ipsec_sad_create()
|
| /dpdk/doc/guides/prog_guide/ |
| H A D | ipsec_lib.rst | 220 key.v4.dip = rte_cpu_to_be_32(dip_val);
228 By performance reason it is better to keep spi/dip/sip in net byte order
241 key.v4.dip = rte_cpu_to_be_32(necessary_dip);
268 uint32_t dip;
278 uint8_t dip[16];
293 keys[i].v4.dip = ipv4_hdr[i]->dst_addr;
|
| /dpdk/examples/ipsec-secgw/ |
| H A D | sad.h | 116 v4[nb_v4].dip = ipv4->dst_addr; in sad_lookup()
131 memcpy(v6[nb_v6].dip, ipv6->dst_addr, in sad_lookup()
|
| /dpdk/drivers/common/iavf/ |
| H A D | virtchnl_inline_ipsec.h | 436 u32 dip[4]; member
|
| /dpdk/drivers/net/iavf/ |
| H A D | iavf_ipsec_crypto.c | 767 request->ipsec_data.sp_cfg->dip[0] = htonl(v4_dst_addr); in iavf_ipsec_crypto_inbound_security_policy_add()
771 request->ipsec_data.sp_cfg->dip[0] = in iavf_ipsec_crypto_inbound_security_policy_add()
773 request->ipsec_data.sp_cfg->dip[1] = in iavf_ipsec_crypto_inbound_security_policy_add()
775 request->ipsec_data.sp_cfg->dip[2] = in iavf_ipsec_crypto_inbound_security_policy_add()
777 request->ipsec_data.sp_cfg->dip[3] = in iavf_ipsec_crypto_inbound_security_policy_add()
|
| /dpdk/drivers/net/hinic/base/ |
| H A D | hinic_pmd_niccfg.h | 696 struct pa_u32_s dip; /* 32bit */ member
|
| /dpdk/drivers/crypto/mvsam/ |
| H A D | rte_mrvl_pmd.c | 540 sess->sam_sess_params.u.ipsec.tunnel.u.ipv4.dip = in mrvl_ipsec_set_session_parameters()
|