Home
last modified time | relevance | path

Searched refs:dp2 (Results 1 – 5 of 5) sorted by relevance

/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_neon.h75 uint16x8_t dp2) in port_groupx4() argument
85 dp1 = vceqq_u16(dp1, dp2); in port_groupx4()
146 uint16x8_t dp1, dp2; in send_packets_multi() local
163 dp2 = vld1q_u16(&dst_port[j - FWDSTEP + 1]); in send_packets_multi()
164 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
170 dp1 = vextq_u16(dp2, dp1, FWDSTEP - 1); in send_packets_multi()
176 dp2 = vextq_u16(dp1, dp1, 1); in send_packets_multi()
177 dp2 = vsetq_lane_u16(vgetq_lane_u16(dp2, 2), dp2, 3); in send_packets_multi()
178 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
H A Dl3fwd_altivec.h95 vector unsigned short dp2) in port_groupx4() argument
104 v = vec_any_eq(dp1, dp2); in port_groupx4()
168 vector unsigned short dp1, dp2; in send_packets_multi() local
185 dp2 = *((vector unsigned short *) in send_packets_multi()
187 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
193 dp1 = vec_sro(dp2, (vector unsigned char) { in send_packets_multi()
201 dp2 = vec_perm(dp1, (vector unsigned short){}, in send_packets_multi()
203 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
H A Dl3fwd_sse.h74 port_groupx4(uint16_t pn[FWDSTEP + 1], uint16_t *lp, __m128i dp1, __m128i dp2) in port_groupx4() argument
83 dp1 = _mm_cmpeq_epi16(dp1, dp2); in port_groupx4()
142 __m128i dp1, dp2; in send_packets_multi() local
159 dp2 = _mm_loadu_si128((__m128i *) in send_packets_multi()
161 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
167 dp1 = _mm_srli_si128(dp2, (FWDSTEP - 1) * in send_packets_multi()
174 dp2 = _mm_shufflelo_epi16(dp1, 0xf9); in send_packets_multi()
175 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c1564 port_groupx4(uint16_t pn[FWDSTEP + 1], uint16_t *lp, __m128i dp1, __m128i dp2) in port_groupx4() argument
1676 dp1 = _mm_cmpeq_epi16(dp1, dp2); in port_groupx4()
1770 __m128i dp1, dp2; in process_burst() local
1787 dp2 = _mm_loadu_si128( in process_burst()
1789 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in process_burst()
1795 dp1 = _mm_srli_si128(dp2, (FWDSTEP - 1) * in process_burst()
1802 dp2 = _mm_shufflelo_epi16(dp1, 0xf9); in process_burst()
1803 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in process_burst()
/f-stack/dpdk/drivers/common/octeontx2/hw/
H A Dotx2_npc.h287 uint16_t dp2; member