| /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()
89 int32x4_t dip; in l3fwd_lpm_process_packets() local
106 processx4_step1(&pkts_burst[j], &dip, &ipv4_flag); in l3fwd_lpm_process_packets()
107 processx4_step2(qconf, dip, ipv4_fla in l3fwd_lpm_process_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_process_packets() local
95 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_process_packets()
99 processx4_step2(qconf, dip[ in l3fwd_lpm_process_packets()
[all...] |
| 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_process_packets() local
109 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_process_packets()
113 processx4_step2(qconf, dip[ in l3fwd_lpm_process_packets()
[all...] |
| /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, in ip4_lookup_node_process_vec()
[all...] |
| 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/examples/ipsec-secgw/ |
| H A D | ipsec_lpm_neon.h | 17 processx4_step1(struct rte_mbuf *pkt[FWDSTEP], int32x4_t *dip, in processx4_step1()
38 dip[0] = vld1q_s32(dst);
45 processx4_step2(struct rt_ctx *rt_ctx, int32x4_t dip, uint64_t inline_flag, in processx4_step2()
52 dip = vreinterpretq_s32_u8(vrev32q_u8(vreinterpretq_u8_s32(dip))); in processx4_step2()
56 rte_lpm_lookupx4((struct rte_lpm *)rt_ctx, dip, dst.u32, in processx4_step2()
64 dst.x = dip; in processx4_step2()
183 int32x4_t dip; in route4_pkts_neon()
190 processx4_step1(&pkts[i], &dip, &inline_flag); in route4_pkts_neon()
191 processx4_step2(rt_ctx, dip, inline_fla in route4_pkts_neon()
15 processx4_step1(struct rte_mbuf * pkt[FWDSTEP],int32x4_t * dip,uint64_t * inline_flag) processx4_step1() argument
43 processx4_step2(struct rt_ctx * rt_ctx,int32x4_t dip,uint64_t inline_flag,struct rte_mbuf * pkt[FWDSTEP],uint16_t dprt[FWDSTEP]) processx4_step2() argument
182 int32x4_t dip; route4_pkts_neon() local
[all...] |
| H A D | sad.h | 119 v4[nb_v4].dip = ipv4->dst_addr; in sad_lookup()
134 v6[nb_v6].dip = ipv6->dst_addr; in sad_lookup()
|
| /dpdk/lib/ipsec/ |
| H A D | rte_ipsec_sad.h | 36 uint32_t dip;
42 struct rte_ipv6_addr dip;
53 /** Flag to create SAD with ipv6 dip and sip addresses */
79 * key type (spi only/spi+dip/spi+dip+sip)
102 * key type (spi only/spi+dip/spi+dip+sip)
35 uint32_t dip; global() member
41 uint8_t dip[16]; global() 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/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 | 538 sess->sam_sess_params.u.ipsec.tunnel.u.ipv4.dip = in mrvl_ipsec_set_session_parameters()
|