Home
last modified time | relevance | path

Searched refs:dst (Results 1 – 25 of 196) sorted by relevance

12345678

/dpdk/lib/eal/arm/include/
H A Drte_memcpy_32.h27 rte_mov16(uint8_t *dst, const uint8_t *src) in rte_mov16() argument
29 vst1q_u8(dst, vld1q_u8(src)); in rte_mov16()
33 rte_mov32(uint8_t *dst, const uint8_t *src) in rte_mov32() argument
38 : "+r" (src), "+r" (dst) in rte_mov32()
43 rte_mov48(uint8_t *dst, const uint8_t *src) in rte_mov48() argument
50 : "+r" (src), "+r" (dst) in rte_mov48()
56 rte_mov64(uint8_t *dst, const uint8_t *src) in rte_mov64() argument
63 : "+r" (src), "+r" (dst) in rte_mov64()
69 rte_mov128(uint8_t *dst, const uint8_t *src) in rte_mov128() argument
81 : "+r" (src), "+r" (dst) in rte_mov128()
88 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
122 rte_memcpy(dst,src,n) global() argument
129 rte_memcpy_func(void * dst,const void * src,size_t n) rte_memcpy_func() argument
[all...]
H A Drte_memcpy_64.h48 #define RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, src) \ argument
51 /* Both dst and src unalignment will be treated as unaligned copy */
52 #define RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, src) \
53 (((uintptr_t)(dst) | (uintptr_t)(src)) & RTE_ARM64_MEMCPY_ALIGN_MASK)
62 #define USE_ALIGNED_RTE_MEMCPY(dst, src, n) \ argument
63 (!RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, src) && \
66 #define USE_ALIGNED_RTE_MEMCPY(dst, src, n) \
67 (!RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, src))
70 #define USE_UNALIGNED_RTE_MEMCPY(dst, src, n) \ argument
71 (RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, sr
82 USE_RTE_MEMCPY(dst,src,n) global() argument
101 rte_mov16(uint8_t * dst,const uint8_t * src) rte_mov16() argument
109 rte_mov32(uint8_t * dst,const uint8_t * src) rte_mov32() argument
119 rte_mov48(uint8_t * dst,const uint8_t * src) rte_mov48() argument
130 rte_mov64(uint8_t * dst,const uint8_t * src) rte_mov64() argument
143 rte_mov128(uint8_t * dst,const uint8_t * src) rte_mov128() argument
165 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
172 rte_memcpy_lt16(uint8_t * dst,const uint8_t * src,size_t n) rte_memcpy_lt16() argument
193 rte_memcpy_ge16_lt128(uint8_t * dst,const uint8_t * src,size_t n) rte_memcpy_ge16_lt128() argument
222 rte_memcpy_ge128(uint8_t * dst,const uint8_t * src,size_t n) rte_memcpy_ge128() argument
246 rte_memcpy_ge16_lt64(uint8_t * dst,const uint8_t * src,size_t n) rte_memcpy_ge16_lt64() argument
263 rte_memcpy_ge64(uint8_t * dst,const uint8_t * src,size_t n) rte_memcpy_ge64() argument
286 rte_memcpy(void * dst,const void * src,size_t n) rte_memcpy() argument
307 rte_memcpy(void * dst,const void * src,size_t n) rte_memcpy() argument
[all...]
H A Drte_atomic_64.h52 cas_op_name(rte_int128_t *dst, rte_int128_t *old, rte_int128_t updated) \
64 op_string " %[old0], %[old1], %[upd0], %[upd1], [%[dst]]" \
69 [dst] "r" (dst) \
77 cas_op_name(rte_int128_t *dst, rte_int128_t *old, rte_int128_t updated) \
80 op_string " %[old], %H[old], %[upd], %H[upd], [%[dst]]" \
82 : [upd] "r"(updated.int128), [dst] "r"(dst) \
97 rte_atomic128_cmp_exchange(rte_int128_t *dst, rte_int128_t *exp, in rte_atomic128_cmp_exchange() argument
120 __cas_128_relaxed(dst, ex in rte_atomic128_cmp_exchange()
146 __LOAD_128(op_string,src,dst) rte_atomic128_cmp_exchange() argument
161 __STORE_128(op_string,dst,src,ret) rte_atomic128_cmp_exchange() argument
[all...]
H A Drte_pause_64.h54 #define __RTE_ARM_LOAD_EXC_8(src, dst, memorder) { \
57 : [tmp] "=&r" (dst) \
62 : [tmp] "=&r" (dst) \
73 #define __RTE_ARM_LOAD_EXC_16(src, dst, memorder) { \
76 : [tmp] "=&r" (dst) \
81 : [tmp] "=&r" (dst) \
92 #define __RTE_ARM_LOAD_EXC_32(src, dst, memorder) { \
95 : [tmp] "=&r" (dst) \
100 : [tmp] "=&r" (dst) \
111 #define __RTE_ARM_LOAD_EXC_64(src, dst, memorde
44 __RTE_ARM_LOAD_EXC_8(src,dst,memorder) global() argument
63 __RTE_ARM_LOAD_EXC_16(src,dst,memorder) global() argument
82 __RTE_ARM_LOAD_EXC_32(src,dst,memorder) global() argument
101 __RTE_ARM_LOAD_EXC_64(src,dst,memorder) global() argument
120 __RTE_ARM_LOAD_EXC_128(src,dst,memorder) global() argument
136 __RTE_ARM_LOAD_EXC(src,dst,memorder,size) global() argument
[all...]
/dpdk/lib/eal/ppc/include/
H A Drte_memcpy.h32 rte_mov16(uint8_t *dst, const uint8_t *src) in rte_mov16() argument
34 vec_vsx_st(vec_vsx_ld(0, src), 0, dst); in rte_mov16()
38 rte_mov32(uint8_t *dst, const uint8_t *src) in rte_mov32() argument
40 vec_vsx_st(vec_vsx_ld(0, src), 0, dst); in rte_mov32()
41 vec_vsx_st(vec_vsx_ld(16, src), 16, dst); in rte_mov32()
45 rte_mov48(uint8_t *dst, const uint8_t *src) in rte_mov48() argument
47 vec_vsx_st(vec_vsx_ld(0, src), 0, dst); in rte_mov48()
48 vec_vsx_st(vec_vsx_ld(16, src), 16, dst); in rte_mov48()
49 vec_vsx_st(vec_vsx_ld(32, src), 32, dst); in rte_mov48()
53 rte_mov64(uint8_t *dst, cons argument
62 rte_mov128(uint8_t * dst,const uint8_t * src) rte_mov128() argument
75 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
81 rte_memcpy(dst,src,n) global() argument
88 rte_memcpy_func(void * dst,const void * src,size_t n) rte_memcpy_func() argument
[all...]
/dpdk/lib/eal/x86/include/
H A Drte_memcpy.h46 * @param dst
56 rte_memcpy(void *dst, const void *src, size_t n);
64 rte_mov15_or_less(void *dst, const void *src, size_t n) in rte_mov15_or_less() argument
80 void *ret = dst; in rte_mov15_or_less()
82 ((struct rte_uint64_alias *)dst)->val = in rte_mov15_or_less()
85 dst = (uint64_t *)dst + 1; in rte_mov15_or_less()
88 ((struct rte_uint32_alias *)dst)->val = in rte_mov15_or_less()
91 dst = (uint32_t *)dst in rte_mov15_or_less()
109 rte_mov16(uint8_t * dst,const uint8_t * src) rte_mov16() argument
122 rte_mov32(uint8_t * dst,const uint8_t * src) rte_mov32() argument
140 rte_mov64(uint8_t * dst,const uint8_t * src) rte_mov64() argument
158 rte_mov128(uint8_t * dst,const uint8_t * src) rte_mov128() argument
169 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
188 rte_mov128blocks(uint8_t * dst,const uint8_t * src,size_t n) rte_mov128blocks() argument
208 rte_mov512blocks(uint8_t * dst,const uint8_t * src,size_t n) rte_mov512blocks() argument
236 rte_memcpy_generic(void * dst,const void * src,size_t n) rte_memcpy_generic() argument
357 rte_mov128blocks(uint8_t * dst,const uint8_t * src,size_t n) rte_mov128blocks() argument
385 rte_memcpy_generic(void * dst,const void * src,size_t n) rte_memcpy_generic() argument
493 MOVEUNALIGNED_LEFT47_IMM(dst,src,len,offset) global() argument
554 MOVEUNALIGNED_LEFT47(dst,src,len,offset) global() argument
577 rte_memcpy_generic(void * dst,const void * src,size_t n) rte_memcpy_generic() argument
700 rte_memcpy_aligned(void * dst,const void * src,size_t n) rte_memcpy_aligned() argument
752 rte_memcpy(void * dst,const void * src,size_t n) rte_memcpy() argument
[all...]
H A Drte_atomic.h116 rte_atomic16_cmpset(volatile uint16_t *dst, uint16_t exp, uint16_t src) in rte_atomic16_cmpset()
122 "cmpxchgw %[src], %[dst];" in rte_atomic16_cmpset()
125 [dst] "=m" (*dst)
128 "m" (*dst) in rte_atomic16_exchange()
134 rte_atomic16_exchange(volatile uint16_t *dst, uint16_t val) in rte_atomic16_exchange()
139 : "=r" (val), "=m" (*dst) in rte_atomic16_test_and_set()
140 : "0" (val), "m" (*dst) in rte_atomic16_test_and_set()
202 rte_atomic32_cmpset(volatile uint32_t *dst, uint32_t exp, uint32_t src) in rte_atomic32_cmpset()
208 "cmpxchgl %[src], %[dst];" in rte_atomic32_cmpset()
108 rte_atomic16_cmpset(volatile uint16_t * dst,uint16_t exp,uint16_t src) rte_atomic16_cmpset() argument
126 rte_atomic16_exchange(volatile uint16_t * dst,uint16_t val) rte_atomic16_exchange() argument
194 rte_atomic32_cmpset(volatile uint32_t * dst,uint32_t exp,uint32_t src) rte_atomic32_cmpset() argument
212 rte_atomic32_exchange(volatile uint32_t * dst,uint32_t val) rte_atomic32_exchange() argument
[all...]
H A Drte_atomic_64.h27 rte_atomic64_cmpset(volatile uint64_t *dst, uint64_t exp, uint64_t src) in rte_atomic64_cmpset() argument
37 [dst] "=m" (*dst) in rte_atomic64_cmpset()
40 "m" (*dst) in rte_atomic64_cmpset()
47 rte_atomic64_exchange(volatile uint64_t *dst, uint64_t val) in rte_atomic64_exchange() argument
52 : "=r" (val), "=m" (*dst) in rte_atomic64_exchange()
53 : "0" (val), "m" (*dst) in rte_atomic64_exchange()
186 rte_atomic128_cmp_exchange(rte_int128_t *dst, in rte_atomic128_cmp_exchange() argument
202 : [dst] "=m" (dst->val[0]), in rte_atomic128_cmp_exchange()
210 "m" (dst->val[0]) in rte_atomic128_cmp_exchange()
/dpdk/drivers/common/dpaax/caamflib/rta/
H A Dmove_cmd.h80 uint64_t dst, uint16_t dst_offset,
88 uint16_t src_offset, uint64_t dst, in rta_move() argument
122 ret = set_move_offset(program, src, src_offset, dst, dst_offset, in rta_move()
164 ret = __rta_map_opcode((uint32_t)dst, move_dst_table, in rta_move()
232 uint64_t dst, uint16_t dst_offset, in set_move_offset() argument
238 if (dst == DESCBUF) { in set_move_offset()
241 } else if ((dst == KEY1) || (dst == KEY2)) { in set_move_offset()
255 if ((dst == MATH0) || (dst == MATH1) || in set_move_offset()
256 (dst == MATH2) || (dst == MATH3)) { in set_move_offset()
258 } else if (((dst == OFIFO) || (dst == ALTSOURCE)) && in set_move_offset()
[all …]
/dpdk/examples/ipsec-secgw/
H A Dep0.cfg14 sp ipv4 out esp protect 5 pri 1 dst 192.168.105.0/24 sport 0:65535 dport 0:65535
15 sp ipv4 out esp protect 6 pri 1 dst 192.168.106.0/24 sport 0:65535 dport 0:65535
16 sp ipv4 out esp protect 10 pri 1 dst 192.168.175.0/24 sport 0:65535 dport 0:65535
17 sp ipv4 out esp protect 11 pri 1 dst 192.168.176.0/24 sport 0:65535 dport 0:65535
18 sp ipv4 out esp protect 15 pri 1 dst 192.168.200.0/24 sport 0:65535 dport 0:65535
19 sp ipv4 out esp protect 16 pri 1 dst 192.168.201.0/24 sport 0:65535 dport 0:65535
20 sp ipv4 out esp protect 25 pri 1 dst 192.168.55.0/24 sport 0:65535 dport 0:65535
21 sp ipv4 out esp protect 26 pri 1 dst 192.168.56.0/24 sport 0:65535 dport 0:65535
22 sp ipv4 out esp bypass pri 1 dst 192.168.240.0/24 sport 0:65535 dport 0:65535
23 sp ipv4 out esp bypass pri 1 dst 192.168.241.0/24 sport 0:65535 dport 0:65535
[all …]
H A Dep1.cfg14 sp ipv4 in esp protect 5 pri 1 dst 192.168.105.0/24 sport 0:65535 dport 0:65535
15 sp ipv4 in esp protect 6 pri 1 dst 192.168.106.0/24 sport 0:65535 dport 0:65535
16 sp ipv4 in esp protect 10 pri 1 dst 192.168.175.0/24 sport 0:65535 dport 0:65535
17 sp ipv4 in esp protect 11 pri 1 dst 192.168.176.0/24 sport 0:65535 dport 0:65535
18 sp ipv4 in esp protect 15 pri 1 dst 192.168.200.0/24 sport 0:65535 dport 0:65535
19 sp ipv4 in esp protect 16 pri 1 dst 192.168.201.0/24 sport 0:65535 dport 0:65535
20 sp ipv4 in esp protect 25 pri 1 dst 192.168.55.0/24 sport 0:65535 dport 0:65535
21 sp ipv4 in esp protect 26 pri 1 dst 192.168.56.0/24 sport 0:65535 dport 0:65535
22 sp ipv4 in esp bypass pri 1 dst 192.168.240.0/24 sport 0:65535 dport 0:65535
23 sp ipv4 in esp bypass pri 1 dst 192.168.241.0/24 sport 0:65535 dport 0:65535
[all …]
/dpdk/lib/eal/include/
H A Drte_string_fns.h61 rte_strlcpy(char *dst, const char *src, size_t size) in rte_strlcpy() argument
63 return (size_t)snprintf(dst, size, "%s", src); in rte_strlcpy()
72 rte_strlcat(char *dst, const char *src, size_t size) in rte_strlcat() argument
74 size_t l = strnlen(dst, size); in rte_strlcat()
76 return l + rte_strlcpy(&dst[l], src, size - l); in rte_strlcat()
87 #define strlcpy(dst, src, size) rte_strlcpy(dst, src, size)
88 #define strlcat(dst, src, size) rte_strlcat(dst, src, size)
96 #define strlcpy(dst, sr
83 strlcpy(dst,src,size) global() argument
84 strlcat(dst,src,size) global() argument
92 strlcpy(dst,src,size) global() argument
93 strlcat(dst,src,size) global() argument
[all...]
/dpdk/lib/eal/riscv/include/
H A Drte_memcpy.h22 rte_mov16(uint8_t *dst, const uint8_t *src) in rte_mov16() argument
24 memcpy(dst, src, 16); in rte_mov16()
28 rte_mov32(uint8_t *dst, const uint8_t *src) in rte_mov32() argument
30 memcpy(dst, src, 32); in rte_mov32()
34 rte_mov48(uint8_t *dst, const uint8_t *src) in rte_mov48() argument
36 memcpy(dst, src, 48); in rte_mov48()
40 rte_mov64(uint8_t *dst, const uint8_t *src) in rte_mov64() argument
42 memcpy(dst, src, 64); in rte_mov64()
46 rte_mov128(uint8_t *dst, const uint8_t *src) in rte_mov128() argument
48 memcpy(dst, sr in rte_mov128()
52 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
[all...]
/dpdk/lib/eal/loongarch/include/
H A Drte_memcpy.h20 rte_mov16(uint8_t *dst, const uint8_t *src) in rte_mov16() argument
22 memcpy(dst, src, 16); in rte_mov16()
26 rte_mov32(uint8_t *dst, const uint8_t *src) in rte_mov32() argument
28 memcpy(dst, src, 32); in rte_mov32()
32 rte_mov48(uint8_t *dst, const uint8_t *src) in rte_mov48() argument
34 memcpy(dst, src, 48); in rte_mov48()
38 rte_mov64(uint8_t *dst, const uint8_t *src) in rte_mov64() argument
40 memcpy(dst, src, 64); in rte_mov64()
44 rte_mov128(uint8_t *dst, const uint8_t *src) in rte_mov128() argument
46 memcpy(dst, sr in rte_mov128()
50 rte_mov256(uint8_t * dst,const uint8_t * src) rte_mov256() argument
[all...]
/dpdk/examples/ipsec-secgw/test/
H A Dtun_aesgcm_defs.sh14 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
16 tmpl src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
20 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
22 tmpl src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
49 tmpl src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
55 tmpl src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
[all …]
H A Dtun_3descbc_sha1_defs.sh14 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
16 tmpl src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
20 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
22 tmpl src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
49 tmpl src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
55 tmpl src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
[all …]
H A Dtun_aescbc_sha1_defs.sh14 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
16 tmpl src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
20 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
22 tmpl src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
49 tmpl src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
55 tmpl src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
[all …]
H A Dtun_aesctr_sha1_defs.sh14 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
16 tmpl src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
20 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
22 tmpl src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
49 tmpl src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
55 tmpl src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
[all …]
H A Ddata_rxtx.sh8 dst=$1
15 ping -c 1 -s ${i} -M dont ${dst}
21 echo "ERROR: $0 failed for dst=${dst}, sz=${i}"
28 dst=$1
35 ping6 -c 1 -s ${i} -M dont ${dst}
41 echo "ERROR: $0 failed for dst=${dst}, sz=${i}"
48 dst=$1
53 scp ${x} [${dst}]:${x}
54 scp [${dst}]:${x} ${x}.copy1
H A Dtun_aesgcm_common_defs.sh11 sp ipv4 in esp protect 7 pri 2 src ${REMOTE_IPV4}/32 dst ${LOCAL_IPV4}/32 \
16 sp ipv4 out esp protect 7 pri 2 src ${LOCAL_IPV4}/32 dst ${REMOTE_IPV4}/32 \
21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
33 mode ipv4-tunnel src ${REMOTE_IPV4} dst ${LOCAL_IPV4} ${SGW_CFG_XPRM_IN}
37 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
42 mode ipv4-tunnel src ${LOCAL_IPV4} dst ${REMOTE_IPV4} ${SGW_CFG_XPRM_OUT}
46 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6} ${SGW_CFG_XPRM_OUT}
49 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
50 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
[all …]
H A Dtun_aescbc_sha1_common_defs.sh11 sp ipv4 in esp protect 7 pri 2 src ${REMOTE_IPV4}/32 dst ${LOCAL_IPV4}/32 \
16 sp ipv4 out esp protect 7 pri 2 src ${LOCAL_IPV4}/32 dst ${REMOTE_IPV4}/32 \
21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
35 mode ipv4-tunnel src ${REMOTE_IPV4} dst ${LOCAL_IPV4} ${SGW_CFG_XPRM_IN}
41 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
48 mode ipv4-tunnel src ${LOCAL_IPV4} dst ${REMOTE_IPV4} ${SGW_CFG_XPRM_OUT}
54 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6} ${SGW_CFG_XPRM_OUT}
57 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
58 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
[all …]
/dpdk/lib/eal/freebsd/include/
H A Drte_os.h29 #define RTE_CPU_AND(dst, src1, src2) do \
34 CPU_COPY(&tmp, dst); \
36 #define RTE_CPU_OR(dst, src1, src2) do \
41 CPU_COPY(&tmp, dst); \
47 #define RTE_CPU_NOT(dst, src) do \
52 CPU_COPY(&tmp, dst); \
55 #define RTE_CPU_NOT(dst, src) do \
60 CPU_COPY(&tmp, dst); \
69 #define RTE_CPU_NOT(dst, src) do { \
72 CPU_XOR(dst, sr
33 RTE_CPU_AND(dst,src1,src2) global() argument
40 RTE_CPU_OR(dst,src1,src2) global() argument
51 RTE_CPU_NOT(dst,src) global() argument
59 RTE_CPU_NOT(dst,src) global() argument
73 RTE_CPU_NOT(dst,src) global() argument
[all...]
/dpdk/lib/eal/include/generic/
H A Drte_memcpy.h22 * @param dst
28 rte_mov16(uint8_t *dst, const uint8_t *src);
34 * @param dst
40 rte_mov32(uint8_t *dst, const uint8_t *src);
48 * @param dst
54 rte_mov48(uint8_t *dst, const uint8_t *src);
62 * @param dst
68 rte_mov64(uint8_t *dst, const uint8_t *src);
74 * @param dst
80 rte_mov128(uint8_t *dst, cons
[all...]
/dpdk/examples/l3fwd/
H A Dl3fwd_lpm_neon.h23 int32_t dst[FWDSTEP]; in processx4_step1() local
27 dst[0] = ipv4_hdr->dst_addr; in processx4_step1()
32 dst[1] = ipv4_hdr->dst_addr; in processx4_step1()
37 dst[2] = ipv4_hdr->dst_addr; in processx4_step1()
42 dst[3] = ipv4_hdr->dst_addr; in processx4_step1()
45 dip[0] = vld1q_s32(dst); in processx4_step1()
60 rte_xmm_t dst; in processx4_step2() local
66 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, dip, dst.u32, in processx4_step2()
69 vst1_s16((int16_t *)dprt, vqmovn_s32(dst.x)); in processx4_step2()
71 dst in processx4_step2()
[all...]
/dpdk/drivers/dma/cnxk/
H A Dcnxk_dmadev_fp.c14 __dpi_cpy_scalar(uint64_t *src, uint64_t *dst, uint8_t n) in __dpi_cpy_scalar() argument
19 dst[i] = src[i]; in __dpi_cpy_scalar()
24 __dpi_cpy_vector(uint64_t *src, uint64_t *dst, uint8_t n) in __dpi_cpy_vector() argument
31 vst1q_u64(&dst[i], vec); in __dpi_cpy_vector()
36 __dpi_cpy_vector_sg(const struct rte_dma_sge *src, uint64_t *dst, uint16_t n) in __dpi_cpy_vector_sg() argument
46 vst1q_u64(dst, vec); in __dpi_cpy_vector_sg()
47 dst += 2; in __dpi_cpy_vector_sg()
52 __dpi_cpy_vector_sg_lmt(const struct rte_dma_sge *src, uint64_t *dst, uint16_t n, uint16_t lmt) in __dpi_cpy_vector_sg_lmt() argument
62 vst1q_u64(dst, vec); in __dpi_cpy_vector_sg_lmt()
63 dst += 2; in __dpi_cpy_vector_sg_lmt()
[all …]

12345678