Home
last modified time | relevance | path

Searched refs:FWDSTEP (Results 1 – 9 of 9) sorted by relevance

/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_lpm_sse.h14 processx4_step1(struct rte_mbuf *pkt[FWDSTEP], in processx4_step1() argument
54 struct rte_mbuf *pkt[FWDSTEP], in processx4_step2() argument
55 uint16_t dprt[FWDSTEP]) in processx4_step2() argument
90 __m128i dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets()
91 uint32_t ipv4_flag[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets()
92 const int32_t k = RTE_ALIGN_FLOOR(nb_rx, FWDSTEP); in l3fwd_lpm_send_packets()
94 for (j = 0; j != k; j += FWDSTEP) in l3fwd_lpm_send_packets()
96 &ipv4_flag[j / FWDSTEP]); in l3fwd_lpm_send_packets()
98 for (j = 0; j != k; j += FWDSTEP) in l3fwd_lpm_send_packets()
99 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
[all …]
H A Dl3fwd_altivec.h18 processx4_step3(struct rte_mbuf *pkt[FWDSTEP], uint16_t dst_port[FWDSTEP]) in processx4_step3() argument
20 vector unsigned int te[FWDSTEP]; in processx4_step3()
21 vector unsigned int ve[FWDSTEP]; in processx4_step3()
22 vector unsigned int *p[FWDSTEP]; in processx4_step3()
98 uint16_t u16[FWDSTEP + 1]; in port_groupx4()
113 pnum->u16[FWDSTEP] = 1; in port_groupx4()
166 k = RTE_ALIGN_FLOOR(nb_rx, FWDSTEP); in send_packets_multi()
178 for (j = FWDSTEP; j != k; j += FWDSTEP) { in send_packets_multi()
186 &dst_port[j - FWDSTEP + 1]); in send_packets_multi()
195 0, 0, 0, (FWDSTEP - 1) * sizeof(dst_port[0])}); in send_packets_multi()
[all …]
H A Dl3fwd_sse.h17 processx4_step3(struct rte_mbuf *pkt[FWDSTEP], uint16_t dst_port[FWDSTEP]) in processx4_step3() argument
19 __m128i te[FWDSTEP]; in processx4_step3()
20 __m128i ve[FWDSTEP]; in processx4_step3()
21 __m128i *p[FWDSTEP]; in processx4_step3()
77 uint16_t u16[FWDSTEP + 1]; in port_groupx4()
93 pnum->u16[FWDSTEP] = 1; in port_groupx4()
140 k = RTE_ALIGN_FLOOR(nb_rx, FWDSTEP); in send_packets_multi()
152 for (j = FWDSTEP; j != k; j += FWDSTEP) { in send_packets_multi()
160 &dst_port[j - FWDSTEP + 1]); in send_packets_multi()
167 dp1 = _mm_srli_si128(dp2, (FWDSTEP - 1) * in send_packets_multi()
[all …]
H A Dl3fwd_lpm_altivec.h16 processx4_step1(struct rte_mbuf *pkt[FWDSTEP], in processx4_step1() argument
60 struct rte_mbuf *pkt[FWDSTEP], in processx4_step2() argument
61 uint16_t dprt[FWDSTEP]) in processx4_step2() argument
104 vector unsigned int dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets()
105 uint32_t ipv4_flag[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets()
108 for (j = 0; j != k; j += FWDSTEP) in l3fwd_lpm_send_packets()
110 &ipv4_flag[j / FWDSTEP]); in l3fwd_lpm_send_packets()
112 for (j = 0; j != k; j += FWDSTEP) in l3fwd_lpm_send_packets()
113 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
114 ipv4_flag[j / FWDSTEP], in l3fwd_lpm_send_packets()
[all …]
H A Dl3fwd_neon.h17 processx4_step3(struct rte_mbuf *pkt[FWDSTEP], uint16_t dst_port[FWDSTEP]) in processx4_step3() argument
19 uint32x4_t te[FWDSTEP]; in processx4_step3()
20 uint32x4_t ve[FWDSTEP]; in processx4_step3()
21 uint32_t *p[FWDSTEP]; in processx4_step3()
78 uint16_t u16[FWDSTEP + 1]; in port_groupx4()
96 pnum->u16[FWDSTEP] = 1; in port_groupx4()
144 k = RTE_ALIGN_FLOOR(nb_rx, FWDSTEP); in send_packets_multi()
156 for (j = FWDSTEP; j != k; j += FWDSTEP) { in send_packets_multi()
163 dp2 = vld1q_u16(&dst_port[j - FWDSTEP + 1]); in send_packets_multi()
170 dp1 = vextq_u16(dp2, dp1, FWDSTEP - 1); in send_packets_multi()
[all …]
H A Dl3fwd_lpm_neon.h17 processx4_step1(struct rte_mbuf *pkt[FWDSTEP], in processx4_step1() argument
23 int32_t dst[FWDSTEP]; in processx4_step1()
57 struct rte_mbuf *pkt[FWDSTEP], in processx4_step2() argument
58 uint16_t dprt[FWDSTEP]) in processx4_step2() argument
95 const int32_t k = RTE_ALIGN_FLOOR(nb_rx, FWDSTEP); in l3fwd_lpm_send_packets()
96 const int32_t m = nb_rx % FWDSTEP; in l3fwd_lpm_send_packets()
99 for (i = 0; i < FWDSTEP; i++) { in l3fwd_lpm_send_packets()
104 for (j = 0; j != k - FWDSTEP; j += FWDSTEP) { in l3fwd_lpm_send_packets()
105 for (i = 0; i < FWDSTEP; i++) { in l3fwd_lpm_send_packets()
107 pkts_burst[j + i + FWDSTEP], in l3fwd_lpm_send_packets()
[all …]
H A Dl3fwd_common.h64 #define GRPSZ (1 << FWDSTEP)
210 switch (n % FWDSTEP) { in send_packetsx4()
240 switch (len % FWDSTEP) { in send_packetsx4()
H A Dl3fwd.h44 #define FWDSTEP 4 macro
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c183 #define FWDSTEP 4 macro
703 switch (n % FWDSTEP) { in send_packetsx4()
733 switch (len % FWDSTEP) { in send_packetsx4()
1452 uint16_t dprt[FWDSTEP]) in processx4_step2() argument
1483 processx4_step3(struct rte_mbuf *pkt[FWDSTEP], uint16_t dst_port[FWDSTEP]) in processx4_step3() argument
1485 __m128i te[FWDSTEP]; in processx4_step3()
1486 __m128i ve[FWDSTEP]; in processx4_step3()
1487 __m128i *p[FWDSTEP]; in processx4_step3()
1686 pnum->u16[FWDSTEP] = 1; in port_groupx4()
1761 processx4_step2(dip[j / FWDSTEP], ipv4_flag[j / FWDSTEP], in process_burst()
[all …]