Home
last modified time | relevance | path

Searched refs:src (Results 1 – 25 of 202) sorted by relevance

123456789

/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
71 asm volatile ("pld [%0, #64]" : : "r" (src)); 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.h47 /* Only src unalignment will be treated as unaligned copy */
48 #define RTE_ARM64_MEMCPY_IS_UNALIGNED_COPY(dst, src) \ argument
49 ((uintptr_t)(src) & RTE_ARM64_MEMCPY_ALIGN_MASK)
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 USE_UNALIGNED_RTE_MEMCPY(dst,src,n) global() argument
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_pause_64.h54 #define __RTE_ARM_LOAD_EXC_8(src, dst, memorder) { \
58 : [addr] "r" (src) \
63 : [addr] "r" (src) \ argument
73 #define __RTE_ARM_LOAD_EXC_16(src, dst, memorder) { \
77 : [addr] "r" (src) \
82 : [addr] "r" (src) \ argument
92 #define __RTE_ARM_LOAD_EXC_32(src, dst, memorder) { \
96 : [addr] "r" (src) \
101 : [addr] "r" (src) \ argument
111 #define __RTE_ARM_LOAD_EXC_64(src, ds
44 __RTE_ARM_LOAD_EXC_8(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, const uint8_t *src) in rte_mov64() 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.h48 * @param src
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
83 ((const struct rte_uint64_alias *)src)->val; in rte_mov15_or_less()
84 src = (const uint64_t *)src + 1; in rte_mov15_or_less()
89 ((const struct rte_uint32_alias *)src)->val; in rte_mov15_or_less()
90 src = (const uint32_t *)src + 1; in rte_mov15_or_less()
95 ((const struct rte_uint16_alias *)src) 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...]
/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
76 return l + rte_strlcpy(&dst[l], src, size - l); in rte_strlcat()
77 return l + strlen(src); 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, src, siz
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
134 rte_str_skip_leading_spaces(const char * src) rte_str_skip_leading_spaces() argument
[all...]
/dpdk/lib/eal/freebsd/
H A Deal_interrupts.c88 struct rte_intr_source *src; in rte_intr_callback_register() local
105 TAILQ_FOREACH(src, &intr_sources, next) { in rte_intr_callback_register()
106 if (rte_intr_fd_get(src->intr_handle) == rte_intr_fd_get(intr_handle)) in rte_intr_callback_register()
115 if (src != NULL && in rte_intr_callback_register()
116 rte_intr_type_get(src->intr_handle) == RTE_INTR_HANDLE_ALARM && in rte_intr_callback_register()
117 !TAILQ_EMPTY(&src->callbacks)) { in rte_intr_callback_register()
132 if (src == NULL) { in rte_intr_callback_register()
133 src = calloc(1, sizeof(*src)); in rte_intr_callback_register()
134 if (src == NULL) { in rte_intr_callback_register()
139 src->intr_handle = rte_intr_instance_dup(intr_handle); in rte_intr_callback_register()
[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, src, 12 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, src, 12 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 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}
67 sp ipv4 in esp protect 6 pri 2 src ${REMOTE_IPV4}/32 dst ${LOCAL_IPV4}/32 \
72 sp ipv4 out esp protect 6 pri 2 src ${LOCAL_IPV4}/32 dst ${REMOTE_IPV4}/32 \
[all …]
/dpdk/drivers/common/dpaax/caamflib/rta/
H A Dstore_cmd.h62 rta_store(struct program *program, uint64_t src, in rta_store() argument
87 if ((flags & SEQ) && ((src == JOBDESCBUF) || (src == SHAREDESCBUF) || in rta_store()
88 (src == JOBDESCBUF_EFF) || in rta_store()
89 (src == SHAREDESCBUF_EFF))) { in rta_store()
108 ret = __rta_map_opcode((uint32_t)src, store_src_table, in rta_store()
120 if ((src == DESCBUF) || (src == JOBDESCBUF) || (src == SHAREDESCBUF) || in rta_store()
121 (src == JOBDESCBUF_EFF) || (src == SHAREDESCBUF_EFF)) { in rta_store()
132 if ((src == JOBDESCBUF) || (src == SHAREDESCBUF) || in rta_store()
133 (src == JOBDESCBUF_EFF) || (src == SHAREDESCBUF_EFF)) in rta_store()
142 __rta_inline_data(program, src, flags & __COPY_MASK, length); in rta_store()
/dpdk/lib/eal/include/generic/
H A Drte_memcpy.h24 * @param src
28 rte_mov16(uint8_t *dst, const uint8_t *src);
36 * @param src
40 rte_mov32(uint8_t *dst, const uint8_t *src);
50 * @param src
54 rte_mov48(uint8_t *dst, const uint8_t *src);
64 * @param src
68 rte_mov64(uint8_t *dst, const uint8_t *src);
76 * @param src
80 rte_mov128(uint8_t *dst, const uint8_t *src);
[all...]
/dpdk/lib/eal/linux/
H A Deal_interrupts.c488 struct rte_intr_source *src; in rte_intr_callback_register() local
513 TAILQ_FOREACH(src, &intr_sources, next) { in rte_intr_callback_register()
514 if (rte_intr_fd_get(src->intr_handle) == rte_intr_fd_get(intr_handle)) { in rte_intr_callback_register()
516 if (TAILQ_EMPTY(&src->callbacks)) in rte_intr_callback_register()
519 TAILQ_INSERT_TAIL(&(src->callbacks), callback, next); in rte_intr_callback_register()
526 if (src == NULL) { in rte_intr_callback_register()
527 src = calloc(1, sizeof(*src)); in rte_intr_callback_register()
528 if (src == NULL) { in rte_intr_callback_register()
534 src->intr_handle = rte_intr_instance_dup(intr_handle); in rte_intr_callback_register()
535 if (src->intr_handle == NULL) { in rte_intr_callback_register()
[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
30 vec = vld1q_u64((const uint64_t *)&src[i]); 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
43 vec = vld1q_u64((const uint64_t *)&src[i]); 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
59 vec = vld1q_u64((const uint64_t *)&src[i]); in __dpi_cpy_vector_sg_lmt()
71 __dpi_cpy_scalar_sg(const struct rte_dma_sge *src, uint64_t *dst, uint16_t n) in __dpi_cpy_scalar_sg() argument
76 *dst++ = src[i].length; in __dpi_cpy_scalar_sg()
[all …]
/dpdk/drivers/common/dpaax/caamflib/
H A Drta.h274 #define MOVE(program, src, src_offset, dst, dst_offset, length, opt) \ argument
275 rta_move(program, __MOVE, src, src_offset, dst, dst_offset, length, opt)
302 #define MOVEB(program, src, src_offset, dst, dst_offset, length, opt) \ argument
303 rta_move(program, __MOVEB, src, src_offset, dst, dst_offset, length, \
331 #define MOVEDW(program, src, src_offset, dst, dst_offset, length, opt) \ argument
332 rta_move(program, __MOVEDW, src, src_offset, dst, dst_offset, length, \
353 #define FIFOLOAD(program, data, src, length, flags) \ argument
354 rta_fifo_load(program, data, src, length, flags)
432 #define KEY(program, key_dst, encrypt_flags, src, length, flags) \ argument
433 rta_key(program, key_dst, encrypt_flags, src, length, flags)
[all …]
/dpdk/app/test/
H A Dtest_ring.c456 test_ring_mem_cmp(void *src, void *dst, unsigned int size) in test_ring_mem_cmp() argument
460 ret = memcmp(src, dst, size); in test_ring_mem_cmp()
462 rte_hexdump(stdout, "src", src, size); in test_ring_mem_cmp()
590 void **src = NULL, **cur_src = NULL, **dst = NULL, **cur_dst = NULL; in test_ring_burst_bulk_tests1() local
606 src = test_ring_calloc(RING_SIZE * 2, esize[i]); in test_ring_burst_bulk_tests1()
607 if (src == NULL) in test_ring_burst_bulk_tests1()
609 test_ring_mem_init(src, RING_SIZE * 2, esize[i]); in test_ring_burst_bulk_tests1()
610 cur_src = src; in test_ring_burst_bulk_tests1()
657 TEST_RING_VERIFY(test_ring_mem_cmp(src, dst, in test_ring_burst_bulk_tests1()
663 rte_free(src); in test_ring_burst_bulk_tests1()
[all …]
/dpdk/lib/pipeline/
H A Drte_swx_pipeline_internal.h732 } src; member
747 } src; member
753 struct instr_operand src; member
800 } src; member
1146 uint8_t *src_struct = (thread)->structs[(ip)->alu.src.struct_id]; \
1147 uint64_t *src64_ptr = (uint64_t *)&src_struct[(ip)->alu.src.offset]; \
1149 uint64_t src64_mask = UINT64_MAX >> (64 - (ip)->alu.src.n_bits); \
1150 uint64_t src = src64 & src64_mask; \
1152 uint64_t result = dst operator src; \
1167 uint8_t *src_struct = (thread)->structs[(ip)->alu.src.struct_id]; \
[all …]
/dpdk/drivers/crypto/bcmfs/
H A Dbcmfs_sym.c28 struct fsattr src, dst, iv, key; in process_crypto_cipher_op() local
31 fsattr_sz(&src) = sym_op->cipher.data.length; in process_crypto_cipher_op()
34 fsattr_va(&src) = rte_pktmbuf_mtod_offset in process_crypto_cipher_op()
44 fsattr_pa(&src) = rte_pktmbuf_iova(mbuf_src); in process_crypto_cipher_op()
58 sess->cipher.op, &src, in process_crypto_cipher_op()
74 struct fsattr src, dst, mac, key, iv; in process_crypto_auth_op() local
76 fsattr_sz(&src) = op->sym->auth.data.length; in process_crypto_auth_op()
77 fsattr_va(&src) = rte_pktmbuf_mtod_offset(mbuf_src, in process_crypto_auth_op()
80 fsattr_pa(&src) = rte_pktmbuf_iova(mbuf_src); in process_crypto_auth_op()
110 &src, in process_crypto_auth_op()
[all …]
/dpdk/doc/guides/tools/
H A Dgraph.rst134 …>>> pkts=[Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2…
135 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
136 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
137 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
138 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
139 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
140 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
141 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
142 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2"),
143 … Ether(dst="FA:09:F9:D7:E0:9D", src="10:70:1d:2f:42:2d")/IP(src="28.0.0.1", dst="10.0.2.2")]
[all …]
/dpdk/examples/fips_validation/
H A Dfips_validation_ccm.c50 parser_dvpt_interim(const char *key, char *src, struct fips_val *val) in parser_dvpt_interim() argument
58 tmp = strstr(src, key); in parser_dvpt_interim()
75 parse_dvpt_ct_hex_str(const char *key, char *src, struct fips_val *val) in parse_dvpt_ct_hex_str() argument
81 ret = parse_uint8_known_len_hex_str(key, src, val); in parse_dvpt_ct_hex_str()
85 src += strlen(key) + val->len * 2; in parse_dvpt_ct_hex_str()
87 ret = parse_uint8_known_len_hex_str("", src, &vec.aead.digest); in parse_dvpt_ct_hex_str()
98 parse_uint8_ccm_aad_str(const char *key, char *src, struct fips_val *val) in parse_uint8_ccm_aad_str() argument
102 src += strlen(key); in parse_uint8_ccm_aad_str()
110 char byte[3] = {src[j * 2], src[j * 2 + 1], '\0'}; in parse_uint8_ccm_aad_str()
223 parser_read_ccm_direction_str(__rte_unused const char *key, char *src, in parser_read_ccm_direction_str() argument
[all …]
/dpdk/lib/eal/freebsd/include/
H A Drte_os.h47 #define RTE_CPU_NOT(dst, src) do \
51 CPU_NAND(&tmp, src); \ argument
55 #define RTE_CPU_NOT(dst, src) do \
59 CPU_ANDNOT(&tmp, src); \ argument
69 #define RTE_CPU_NOT(dst, src) do { \
72 CPU_XOR(dst, src, &tmp); \
73 RTE_CPU_NOT(dst,src) global() argument

123456789