Home
last modified time | relevance | path

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

/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.h96 __vector unsigned short dp2) in port_groupx4() argument
105 v = vec_any_eq(dp1, dp2); in port_groupx4()
169 __vector unsigned short dp1, dp2; in send_packets_multi() local
186 dp2 = *((__vector unsigned short *) in send_packets_multi()
188 lp = port_groupx4(&pnum[j - FWDSTEP], lp, dp1, dp2); in send_packets_multi()
194 dp1 = vec_sro(dp2, (__vector unsigned char) { in send_packets_multi()
202 dp2 = vec_perm(dp1, (__vector unsigned short){}, in send_packets_multi()
204 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()
/dpdk/drivers/common/cnxk/hw/
H A Dnpc.h348 uint16_t dp2; member