Home
last modified time | relevance | path

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

12345678910>>...12

/dpdk/lib/eal/x86/include/
H A Drte_memcpy.h75 dst = (uint64_t *)dst + 1; in rte_mov15_or_less()
81 dst = (uint32_t *)dst + 1; in rte_mov15_or_less()
87 dst = (uint16_t *)dst + 1; in rte_mov15_or_less()
181 dst = dst + 128; in rte_mov128blocks()
213 dst = dst + 512; in rte_mov512blocks()
251 dst = (uint8_t *)dst + 256; in rte_memcpy_generic()
257 dst = (uint8_t *)dst + 128; in rte_memcpy_generic()
294 dst = (uint8_t *)dst + bits; in rte_memcpy_generic()
307 dst = (uint8_t *)dst + bits; in rte_memcpy_generic()
402 dst = (uint8_t *)dst + 128; in rte_mov128blocks()
[all …]
H A Drte_atomic.h102 rte_atomic16_cmpset(volatile uint16_t *dst, uint16_t exp, uint16_t src) in rte_atomic16_cmpset() argument
111 [dst] "=m" (*dst) in rte_atomic16_cmpset()
114 "m" (*dst) in rte_atomic16_cmpset()
120 rte_atomic16_exchange(volatile uint16_t *dst, uint16_t val) in rte_atomic16_exchange() argument
125 : "=r" (val), "=m" (*dst) in rte_atomic16_exchange()
126 : "0" (val), "m" (*dst) in rte_atomic16_exchange()
197 [dst] "=m" (*dst) in rte_atomic32_cmpset()
200 "m" (*dst) in rte_atomic32_cmpset()
206 rte_atomic32_exchange(volatile uint32_t *dst, uint32_t val) in rte_atomic32_exchange() argument
211 : "=r" (val), "=m" (*dst) in rte_atomic32_exchange()
[all …]
/dpdk/lib/eal/arm/include/
H A Drte_memcpy_32.h137 dst = (uint8_t *)dst + 1; in rte_memcpy_func()
142 dst = (uint16_t *)dst + 1; in rte_memcpy_func()
147 dst = (uint32_t *)dst + 1; in rte_memcpy_func()
156 dst = (uint32_t *)dst + 1; in rte_memcpy_func()
192 dst = (uint8_t *)dst + 256; in rte_memcpy_func()
208 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
213 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
218 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
232 dst = (uint8_t *)dst + 16; in rte_memcpy_func()
237 dst = (uint8_t *)dst + 16; in rte_memcpy_func()
[all …]
H A Drte_memcpy_64.h167 rte_mov128(dst, src); in rte_mov256()
188 *dst = *src; in rte_memcpy_lt16()
227 dst += 128; in rte_memcpy_ge128()
249 rte_mov16(dst, src); in rte_memcpy_ge16_lt64()
268 dst += 64; in rte_memcpy_ge64()
290 return dst; in rte_memcpy()
294 return dst; in rte_memcpy()
300 return dst; in rte_memcpy()
311 return dst; in rte_memcpy()
315 return dst; in rte_memcpy()
[all …]
H A Drte_atomic_64.h70 [dst] "r" (dst) \
83 : [upd] "r"(updated.int128), [dst] "r"(dst) \
122 __cas_128_relaxed(dst, exp, desired); in rte_atomic128_cmp_exchange()
124 __cas_128_acquire(dst, exp, desired); in rte_atomic128_cmp_exchange()
126 __cas_128_release(dst, exp, desired); in rte_atomic128_cmp_exchange()
151 : "=&r" (dst.val[0]), \ in rte_atomic128_cmp_exchange()
152 "=&r" (dst.val[1]) \ in rte_atomic128_cmp_exchange()
157 __LOAD_128("ldxp", dst, old) in rte_atomic128_cmp_exchange()
159 __LOAD_128("ldaxp", dst, old) in rte_atomic128_cmp_exchange()
169 "Q" (dst->val[0]) \ in rte_atomic128_cmp_exchange()
[all …]
H A Drte_pause_64.h40 #define __RTE_ARM_LOAD_EXC_16(src, dst, memorder) { \ argument
43 : [tmp] "=&r" (dst) \
48 : [tmp] "=&r" (dst) \
62 : [tmp] "=&r" (dst) \
67 : [tmp] "=&r" (dst) \
81 : [tmp] "=&r" (dst) \
86 : [tmp] "=&r" (dst) \
117 __RTE_ARM_LOAD_EXC_16(src, dst, memorder) \
119 __RTE_ARM_LOAD_EXC_32(src, dst, memorder) \
121 __RTE_ARM_LOAD_EXC_64(src, dst, memorder) \
[all …]
/dpdk/lib/eal/ppc/include/
H A Drte_memcpy.h90 void *ret = dst; in rte_memcpy_func()
96 dst = (uint8_t *)dst + 1; in rte_memcpy_func()
101 dst = (uint16_t *)dst + 1; in rte_memcpy_func()
106 dst = (uint32_t *)dst + 1; in rte_memcpy_func()
143 dst = (uint8_t *)dst + 256; in rte_memcpy_func()
159 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
164 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
169 dst = (uint8_t *)dst + 64; in rte_memcpy_func()
183 dst = (uint8_t *)dst + 16; in rte_memcpy_func()
188 dst = (uint8_t *)dst + 16; in rte_memcpy_func()
[all …]
/dpdk/examples/ipsec-secgw/
H A Dep0.cfg86 dst 172.16.2.5
89 dst 172.16.2.6
120 dst 172.16.1.5
125 dst 172.16.1.7 flow-direction 0 2
145 rt ipv4 dst 172.16.2.5/32 port 0
146 rt ipv4 dst 172.16.2.6/32 port 1
147 rt ipv4 dst 192.168.175.0/24 port 0
148 rt ipv4 dst 192.168.176.0/24 port 1
149 rt ipv4 dst 192.168.240.0/24 port 0
153 rt ipv4 dst 192.168.65.0/24 port 2
[all …]
H A Dep1.cfg83 dst 172.16.2.5
86 dst 172.16.2.6
117 dst 172.16.1.5
134 rt ipv4 dst 172.16.1.5/32 port 0
135 rt ipv4 dst 172.16.1.6/32 port 1
136 rt ipv4 dst 192.168.185.0/24 port 0
137 rt ipv4 dst 192.168.186.0/24 port 1
138 rt ipv4 dst 192.168.245.0/24 port 0
139 rt ipv4 dst 192.168.246.0/24 port 1
142 rt ipv4 dst 192.168.55.0/24 port 2
[all …]
/dpdk/drivers/common/dpaax/caamflib/rta/
H A Dmove_cmd.h241 } 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()
278 (dst == IFIFO) || (dst == PKA)) && in set_move_offset()
289 if ((dst == CONTEXT1) || (dst == CONTEXT2)) { in set_move_offset()
292 (dst == MATH2) || (dst == MATH3)) { in set_move_offset()
314 if ((dst == OFIFO) || (dst == ALTSOURCE)) { in set_move_offset()
323 (dst == IFIFO) || (dst == PKA)) { in set_move_offset()
332 if ((dst != KEY1) && (dst != KEY2)) in set_move_offset()
343 if ((dst == IFIFOAB1) || (dst == IFIFOAB2) || in set_move_offset()
[all …]
/dpdk/lib/eal/include/
H A Drte_string_fns.h59 rte_strlcpy(char *dst, const char *src, size_t size) in rte_strlcpy() argument
61 return (size_t)snprintf(dst, size, "%s", src); in rte_strlcpy()
70 rte_strlcat(char *dst, const char *src, size_t size) in rte_strlcat() argument
72 size_t l = strnlen(dst, size); in rte_strlcat()
74 return l + rte_strlcpy(&dst[l], src, size - l); in rte_strlcat()
81 #define strlcpy(dst, src, size) rte_strlcpy(dst, src, size) argument
82 #define strlcat(dst, src, size) rte_strlcat(dst, src, size) argument
90 #define strlcpy(dst, src, size) rte_strlcpy(dst, src, size) argument
91 #define strlcat(dst, src, size) rte_strlcat(dst, src, size) argument
116 rte_strscpy(char *dst, const char *src, size_t dsize);
/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} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
59 src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
66 src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
82 src ${REMOTE_IPV6} dst ${LOCAL_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} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
59 src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
66 src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
82 src ${REMOTE_IPV6} dst ${LOCAL_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} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
59 src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
66 src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
82 src ${REMOTE_IPV6} dst ${LOCAL_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} \
26 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
32 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
47 src ${REMOTE_IPV4} dst ${LOCAL_IPV4} \
53 src ${LOCAL_IPV4} dst ${REMOTE_IPV4} \
59 src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
66 src ${LOCAL_IPV6} dst ${REMOTE_IPV6} \
82 src ${REMOTE_IPV6} dst ${LOCAL_IPV6} \
[all …]
H A Dtun_aesgcm_common_defs.sh11 sp ipv4 in esp protect 7 pri 2 src ${REMOTE_IPV4}/32 dst ${LOCAL_IPV4}/32 \
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}
49 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
50 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
52 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
53 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
105 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
106 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
108 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[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_aescbc_sha1_common_defs.sh57 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
58 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
60 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
61 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
99 mode ipv4-tunnel src ${REMOTE_IPV4} dst ${LOCAL_IPV4}
105 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6}
112 mode ipv4-tunnel src ${LOCAL_IPV4} dst ${REMOTE_IPV4}
121 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
122 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
124 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
H A Dtun_3descbc_sha1_common_defs.sh61 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
62 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
64 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
65 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
104 mode ipv4-tunnel src ${REMOTE_IPV4} dst ${LOCAL_IPV4}
111 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6}
119 mode ipv4-tunnel src ${LOCAL_IPV4} dst ${REMOTE_IPV4}
129 rt ipv4 dst ${REMOTE_IPV4}/32 port 0
130 rt ipv4 dst ${LOCAL_IPV4}/32 port 1
132 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
/dpdk/drivers/net/ice/base/
H A Dice_bitops.h182 dst[i] = bmp1[i] & bmp2[i]; in ice_and_bitmap()
183 res |= dst[i]; in ice_and_bitmap()
193 dst[i] = (dst[i] & ~mask) | ((bmp1[i] & bmp2[i]) & mask); in ice_and_bitmap()
194 res |= dst[i] & mask; in ice_and_bitmap()
219 dst[i] = bmp1[i] | bmp2[i]; in ice_or_bitmap()
227 dst[i] = (dst[i] & ~mask) | ((bmp1[i] | bmp2[i]) & mask); in ice_or_bitmap()
250 dst[i] = bmp1[i] ^ bmp2[i]; in ice_xor_bitmap()
258 dst[i] = (dst[i] & ~mask) | ((bmp1[i] ^ bmp2[i]) & mask); in ice_xor_bitmap()
289 dst[i] = (dst[i] & ~mask) | ((bmp1[i] & ~bmp2[i]) & mask); in ice_andnot_bitmap()
399 ice_set_bit(i, dst); in ice_bitmap_set()
[all …]
/dpdk/drivers/net/bnxt/tf_ulp/
H A Dulp_utils.c887 ulp_bs_put_msb(dst->data, dst->write_idx, ULP_BLOB_BYTE, in ulp_blob_msb_block_merge()
896 ulp_bs_put_msb(dst->data, dst->write_idx, in ulp_blob_msb_block_merge()
898 dst->write_idx += remaining; in ulp_blob_msb_block_merge()
904 ulp_bs_put_msb(dst->data, dst->write_idx, in ulp_blob_msb_block_merge()
962 ulp_bs_put_msb(dst->data, dst->write_idx, in ulp_blob_append()
964 dst->write_idx += remaining; in ulp_blob_append()
972 ulp_bs_put_msb(dst->data, dst->write_idx, ULP_BLOB_BYTE, in ulp_blob_append()
983 ulp_bs_put_msb(dst->data, dst->write_idx, in ulp_blob_append()
985 dst->write_idx += remaining; in ulp_blob_append()
1003 if ((dst->write_idx + src->write_idx) > dst->bitlen) { in ulp_blob_buffer_copy()
[all …]
/dpdk/lib/eal/include/generic/
H A Drte_atomic.h152 return __sync_bool_compare_and_swap(dst, exp, src); in rte_atomic16_cmpset()
176 rte_atomic16_exchange(volatile uint16_t *dst, uint16_t val) in rte_atomic16_exchange() argument
179 return __atomic_exchange_n(dst, val, __ATOMIC_SEQ_CST); in rte_atomic16_exchange()
181 return __atomic_exchange_2(dst, val, __ATOMIC_SEQ_CST); in rte_atomic16_exchange()
435 return __sync_bool_compare_and_swap(dst, exp, src); in rte_atomic32_cmpset()
462 return __atomic_exchange_n(dst, val, __ATOMIC_SEQ_CST); in rte_atomic32_exchange()
464 return __atomic_exchange_4(dst, val, __ATOMIC_SEQ_CST); in rte_atomic32_exchange()
717 return __sync_bool_compare_and_swap(dst, exp, src); in rte_atomic64_cmpset()
744 return __atomic_exchange_n(dst, val, __ATOMIC_SEQ_CST); in rte_atomic64_exchange()
746 return __atomic_exchange_8(dst, val, __ATOMIC_SEQ_CST); in rte_atomic64_exchange()
[all …]
/dpdk/lib/eal/freebsd/include/
H A Drte_os.h33 #define RTE_CPU_AND(dst, src1, src2) do \ argument
38 CPU_COPY(&tmp, dst); \
40 #define RTE_CPU_OR(dst, src1, src2) do \ argument
45 CPU_COPY(&tmp, dst); \
51 #define RTE_CPU_NOT(dst, src) do \ argument
56 CPU_COPY(&tmp, dst); \
59 #define RTE_CPU_NOT(dst, src) do \ argument
64 CPU_COPY(&tmp, dst); \
73 #define RTE_CPU_NOT(dst, src) do { \ argument
76 CPU_XOR(dst, src, &tmp); \
/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
71 dst.x = dip; in processx4_step2()
73 dst.u32[0], portid); in processx4_step2()
75 dst.u32[1], portid); in processx4_step2()
[all …]
/dpdk/lib/ethdev/
H A Drte_flow.c565 } dst; in rte_flow_conv_item_spec() local
583 size > sizeof(*dst.raw) ? sizeof(*dst.raw) : size); in rte_flow_conv_item_spec()
640 } dst; in rte_flow_conv_action_conf() local
655 size > sizeof(*dst.rss) ? sizeof(*dst.rss) : size); in rte_flow_conv_action_conf()
766 dst -= num; in rte_flow_conv_pattern()
800 ++dst; in rte_flow_conv_pattern()
859 dst -= num; in rte_flow_conv_actions()
871 ++dst; in rte_flow_conv_actions()
912 size > sizeof(*dst) ? sizeof(*dst) : size); in rte_flow_conv_rule()
930 dst->pattern = (void *)((uintptr_t)dst + off); in rte_flow_conv_rule()
[all …]

12345678910>>...12