Home
last modified time | relevance | path

Searched refs:in (Results 1 – 25 of 526) sorted by relevance

12345678910>>...22

/dpdk/lib/eal/include/
H A Drte_trace_point.h365 memcpy(mem, &(in), sizeof(in)); \
381 #define __rte_trace_point_emit(in, type) RTE_SET_USED(in) argument
382 #define rte_trace_point_emit_string(in) RTE_SET_USED(in) argument
388 #define rte_trace_point_emit_i64(in) __rte_trace_point_emit(in, int64_t) argument
390 #define rte_trace_point_emit_i32(in) __rte_trace_point_emit(in, int32_t) argument
392 #define rte_trace_point_emit_i16(in) __rte_trace_point_emit(in, int16_t) argument
393 #define rte_trace_point_emit_u8(in) __rte_trace_point_emit(in, uint8_t) argument
394 #define rte_trace_point_emit_i8(in) __rte_trace_point_emit(in, int8_t) argument
395 #define rte_trace_point_emit_int(in) __rte_trace_point_emit(in, int32_t) argument
396 #define rte_trace_point_emit_long(in) __rte_trace_point_emit(in, long) argument
[all …]
H A Drte_eal_trace.h53 rte_trace_point_emit_u64(in);
59 rte_trace_point_emit_u32(in);
65 rte_trace_point_emit_u16(in);
71 rte_trace_point_emit_u8(in);
77 rte_trace_point_emit_i64(in);
83 rte_trace_point_emit_i32(in);
89 rte_trace_point_emit_i16(in);
95 rte_trace_point_emit_i8(in);
100 RTE_TRACE_POINT_ARGS(int in),
101 rte_trace_point_emit_int(in);
[all …]
H A Drte_trace_point_register.h35 #define __rte_trace_point_emit(in, type) \ argument
37 RTE_BUILD_BUG_ON(sizeof(type) != sizeof(typeof(in))); \
38 __rte_trace_point_emit_field(sizeof(type), RTE_STR(in), \
42 #define rte_trace_point_emit_string(in) \ argument
44 RTE_SET_USED(in); \
46 RTE_STR(in)"[32]", "string_bounded_t"); \
/dpdk/lib/pci/
H A Drte_pci.c22 if (*in == '\0') in get_u8_pciaddr_field()
28 if (*in == ' ' || *in == '-') in get_u8_pciaddr_field()
47 in = get_u8_pciaddr_field(in, &dev_addr->bus, ':'); in pci_bdf_parse()
48 if (in == NULL) in pci_bdf_parse()
50 in = get_u8_pciaddr_field(in, &dev_addr->devid, '.'); in pci_bdf_parse()
53 in = get_u8_pciaddr_field(in, &dev_addr->function, '\0'); in pci_bdf_parse()
69 if (*in == ' ' || *in == '-') in pci_dbdf_parse()
81 in = end + 1; in pci_dbdf_parse()
82 in = get_u8_pciaddr_field(in, &dev_addr->bus, ':'); in pci_dbdf_parse()
85 in = get_u8_pciaddr_field(in, &dev_addr->devid, '.'); in pci_dbdf_parse()
[all …]
/dpdk/app/test/
H A Dtest_meter.c440 enum rte_color in[4], out[4]; in tm_test_srtcm_color_aware_check() local
448 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_GREEN; in tm_test_srtcm_color_aware_check()
460 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_YELLOW; in tm_test_srtcm_color_aware_check()
472 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_RED; in tm_test_srtcm_color_aware_check()
548 enum rte_color in[4], out[4]; in tm_test_trtcm_color_aware_check() local
555 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_GREEN; in tm_test_trtcm_color_aware_check()
563 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_YELLOW; in tm_test_trtcm_color_aware_check()
571 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_RED; in tm_test_trtcm_color_aware_check()
652 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_GREEN; in tm_test_trtcm_rfc4115_color_aware_check()
660 in[0] = in[1] = in[2] = in[3] = RTE_COLOR_YELLOW; in tm_test_trtcm_rfc4115_color_aware_check()
[all …]
H A Dtest_table_acl.c100 (in) = end + 1; \
141 char *s, *sp, *in[CB_FLD_NUM]; in parse_cb_ipv4_rule() local
158 if (in[i] == NULL) in parse_cb_ipv4_rule()
169 in[CB_FLD_SRC_ADDR]); in parse_cb_ipv4_rule()
182 in[CB_FLD_DST_ADDR]); in parse_cb_ipv4_rule()
194 in[CB_FLD_SRC_PORT_RANGE]); in parse_cb_ipv4_rule()
206 in[CB_FLD_DST_PORT_RANGE]); in parse_cb_ipv4_rule()
247 if (in[i] == NULL) in parse_cb_ipv4_rule_del()
258 in[CB_FLD_SRC_ADDR]); in parse_cb_ipv4_rule_del()
271 in[CB_FLD_DST_ADDR]); in parse_cb_ipv4_rule_del()
[all …]
/dpdk/examples/ip_pipeline/examples/
H A Drss.cli64 pipeline PIPELINE0 port in 0 table 0
65 pipeline PIPELINE0 port in 1 table 0
66 pipeline PIPELINE0 port in 2 table 0
67 pipeline PIPELINE0 port in 3 table 0
77 pipeline PIPELINE1 port in 0 table 0
78 pipeline PIPELINE1 port in 1 table 0
79 pipeline PIPELINE1 port in 2 table 0
80 pipeline PIPELINE1 port in 3 table 0
90 pipeline PIPELINE2 port in 0 table 0
91 pipeline PIPELINE2 port in 1 table 0
[all …]
/dpdk/lib/acl/
H A Dacl_run_avx2.h201 uint32_t in[MAX_SEARCHES_SSE8]; in search_avx2x16() local
204 in[0] = GET_NEXT_4BYTES(parms, 0); in search_avx2x16()
205 in[4] = GET_NEXT_4BYTES(parms, 4); in search_avx2x16()
206 in[1] = GET_NEXT_4BYTES(parms, 1); in search_avx2x16()
207 in[5] = GET_NEXT_4BYTES(parms, 5); in search_avx2x16()
208 in[2] = GET_NEXT_4BYTES(parms, 2); in search_avx2x16()
209 in[6] = GET_NEXT_4BYTES(parms, 6); in search_avx2x16()
212 input[0] = _mm256_set_epi32(in[7], in[6], in[5], in[4], in search_avx2x16()
213 in[3], in[2], in[1], in[0]); in search_avx2x16()
224 input[1] = _mm256_set_epi32(in[7], in[6], in[5], in[4], in search_avx2x16()
[all …]
H A Dacl_run_avx512_common.h31 _T_simd addr, in, node_type, r, t; in _F_() local
45 r = _M_I_(srli_epi32)(in, 30); in _F_()
47 t = _M_I_(srli_epi32)(in, 24); in _F_()
371 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_()
372 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_()
374 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_()
375 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_()
377 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_()
378 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_()
380 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_()
[all …]
/dpdk/drivers/common/mlx5/
H A Dmlx5_devx_cmds.c91 rc = mlx5_glue->devx_general_cmd(ctx, in, sizeof(in), out, in mlx5_devx_cmd_register_read()
273 rc = mlx5_glue->devx_obj_query(dcs->obj, in, sizeof(in), out, in mlx5_devx_cmd_flow_counter_query()
478 in, sizeof(in), in mlx5_devx_cmd_query_nic_vport_context()
1289 rq->obj = mlx5_glue->devx_obj_create(ctx, in, sizeof(in), in mlx5_devx_cmd_create_rq()
1341 ret = mlx5_glue->devx_obj_modify(rq->obj, in, sizeof(in), in mlx5_devx_cmd_modify_rq()
1578 if (!in) { in mlx5_devx_cmd_create_rqt()
1632 if (!in) { in mlx5_devx_cmd_modify_rqt()
1712 sq->obj = mlx5_glue->devx_obj_create(ctx, in, sizeof(in), in mlx5_devx_cmd_create_sq()
2258 } in; in mlx5_devx_cmd_modify_qp_state() local
2269 memset(&in, 0, sizeof(in)); in mlx5_devx_cmd_modify_qp_state()
[all …]
/dpdk/app/test-acl/
H A Dmain.c362 char *s, *sp, *in[CB_TRC_NUM]; in parse_cb_ipv4_trace() local
368 if (in[i] == NULL) in parse_cb_ipv4_trace()
407 *end = in; in parse_ipv6_addr()
445 char *s, *sp, *in[CB_TRC_NUM]; in parse_cb_ipv6_trace() local
451 if (in[i] == NULL) in parse_cb_ipv6_trace()
598 if (in[i] == NULL) in parse_cb_ipv6_rule()
607 in[CB_FLD_SRC_ADDR]); in parse_cb_ipv6_rule()
615 in[CB_FLD_DST_ADDR]); in parse_cb_ipv6_rule()
693 if (in[i] == NULL) in parse_cb_ipv4_rule()
704 in[CB_FLD_SRC_ADDR]); in parse_cb_ipv4_rule()
[all …]
/dpdk/drivers/regex/mlx5/
H A Dmlx5_regex_devx.c20 uint32_t in[MLX5_ST_SZ_DW(set_regexp_params_in)] = {0}; in mlx5_devx_regex_rules_program() local
23 MLX5_SET(set_regexp_params_in, in, opcode, MLX5_CMD_SET_REGEX_PARAMS); in mlx5_devx_regex_rules_program()
24 MLX5_SET(set_regexp_params_in, in, engine_id, engine); in mlx5_devx_regex_rules_program()
25 MLX5_SET(set_regexp_params_in, in, regexp_params.rof_mkey, rof_mkey); in mlx5_devx_regex_rules_program()
26 MLX5_SET(set_regexp_params_in, in, regexp_params.rof_size, rof_size); in mlx5_devx_regex_rules_program()
27 MLX5_SET64(set_regexp_params_in, in, regexp_params.rof_mkey_va, in mlx5_devx_regex_rules_program()
29 MLX5_SET(set_regexp_params_in, in, field_select.rof_mkey, 1); in mlx5_devx_regex_rules_program()
30 ret = mlx5_glue->devx_general_cmd(ctx, in, sizeof(in), out, in mlx5_devx_regex_rules_program()
/dpdk/doc/guides/rel_notes/
H A Drelease_22_07.rst30 * **Add a title in the past tense with a full stop.**
44 Suggested order in release notes items:
60 Added an API which can get the number of in-flight packets in
71 * Added support for RSS RETA configure in DCF mode.
72 * Added support for RSS HASH configure in DCF mode.
73 * Added support for MTU configure in DCF mode.
75 * Added support for MAC configuration in DCF mode.
114 in the past tense.
127 which was announced in the previous releases and made in this release.
143 which was announced in the previous releases and made in this release.
[all …]
/dpdk/drivers/common/cnxk/
H A Droc_io_generic.h102 roc_lmt_mov(void *out, const void *in, const uint32_t lmtext) in roc_lmt_mov() argument
104 PLT_SET_USED(in); in roc_lmt_mov()
110 roc_lmt_mov64(void *out, const void *in) in roc_lmt_mov64() argument
113 PLT_SET_USED(in); in roc_lmt_mov64()
117 roc_lmt_mov_nv(void *out, const void *in, const uint32_t lmtext) in roc_lmt_mov_nv() argument
119 PLT_SET_USED(in); in roc_lmt_mov_nv()
125 roc_lmt_mov_seg(void *out, const void *in, const uint16_t segdw) in roc_lmt_mov_seg() argument
128 PLT_SET_USED(in); in roc_lmt_mov_seg()
133 roc_lmt_mov_one(void *out, const void *in) in roc_lmt_mov_one() argument
136 PLT_SET_USED(in); in roc_lmt_mov_one()
[all …]
H A Droc_io.h158 roc_lmt_mov(void *out, const void *in, const uint32_t lmtext) in roc_lmt_mov() argument
160 volatile const __uint128_t *src128 = (const __uint128_t *)in; in roc_lmt_mov()
173 roc_lmt_mov64(void *out, const void *in) in roc_lmt_mov64() argument
175 volatile const __uint128_t *src128 = (const __uint128_t *)in; in roc_lmt_mov64()
185 roc_lmt_mov_nv(void *out, const void *in, const uint32_t lmtext) in roc_lmt_mov_nv() argument
187 const __uint128_t *src128 = (const __uint128_t *)in; in roc_lmt_mov_nv()
200 roc_lmt_mov_seg(void *out, const void *in, const uint16_t segdw) in roc_lmt_mov_seg() argument
202 volatile const __uint128_t *src128 = (const __uint128_t *)in; in roc_lmt_mov_seg()
211 roc_lmt_mov_one(void *out, const void *in) in roc_lmt_mov_one() argument
213 volatile const __uint128_t *src128 = (const __uint128_t *)in; in roc_lmt_mov_one()
[all …]
/dpdk/examples/l3fwd/
H A Dem_route_parse.c27 em_parse_v6_net(const char *in, uint8_t *v) in em_parse_v6_net() argument
32 rc = inet_pton(AF_INET6, in, v); in em_parse_v6_net()
43 char *s, *sp, *in[CB_FLD_MAX]; in em_parse_v6_rule() local
49 in[i] = strtok_r(s, dlm, &sp); in em_parse_v6_rule()
50 if (in[i] == NULL) in em_parse_v6_rule()
54 rc = em_parse_v6_net(in[CB_FLD_DST_ADDR], v->v6_key.ip_dst); in em_parse_v6_rule()
57 rc = em_parse_v6_net(in[CB_FLD_SRC_ADDR], v->v6_key.ip_src); in em_parse_v6_rule()
68 GET_CB_FIELD(in[CB_FLD_IF_OUT], v->if_out, 0, UINT8_MAX, 0); in em_parse_v6_rule()
77 char *s, *sp, *in[CB_FLD_MAX]; in em_parse_v4_rule() local
83 in[i] = strtok_r(s, dlm, &sp); in em_parse_v4_rule()
[all …]
/dpdk/lib/ethdev/
H A Dversion.map138 # added in 17.11
151 # added in 18.02
158 # added in 18.05
162 # added in 18.11
165 # added in 19.08
168 # added in 19.11
176 # added in 20.02
179 # added in 20.05
222 # added in 20.11
237 # added in 21.02
[all …]
/dpdk/doc/guides/prog_guide/
H A Dtimer_lib.rst30 with all pending timers for a core being maintained in order of timer expiry in a skiplist data str…
31 The skiplist used has ten levels and each entry in the table appears in each level with probability…
32 This means that all entries are present in level 0, 1 in every 4 entries is present at level 1,
33 one in every 16 at level 2 and so on up to level 9.
39 Depending on the timer state, we know if a timer is present in a list or not:
41 * STOPPED: no owner, not in a list
45 * PENDING: owned by a core, present in a list
47 * RUNNING: owned by a core, must not be modified by another core, present in a list
49 Resetting or stopping a timer while it is in a CONFIG or RUNNING state is not allowed.
56 To improve performance in the case where there are entries in the timer list but none of those time…
[all …]
H A Dflow_classify_lib.rst87 * @param[in] cls
89 * @param[in] attr
111 * @param[in] cls
113 * @param[in] attr
138 * @param[in] cls
140 * @param[in] rule
152 * @param[in] cls
154 * @param[in] pkts
158 * @param[in] rule
160 * @param[in] stats
[all …]
H A Dthread_safety_dpdk_functions.rst14 Where this is not possible, then the execution blocks must access the data in a thread- safe manner.
21 Applications operating in the data plane are performance sensitive but
23 The hash, LPM and mempool libraries and RX/TX in the PMD are examples of this.
25 The hash and LPM libraries are, by design, thread unsafe in order to maintain performance.
27 Locking is not needed in all situations, and in both the hash and LPM libraries,
28 lookups of values can be performed in parallel in multiple threads.
47 Outside of the performance sensitive areas described in Section 25.1,
59 It is recommended that DPDK libraries are initialized in the main thread at application startup
60 rather than subsequently in the forwarding threads.
70 The DPDK works almost entirely in Linux user space in polling mode.
[all …]
H A Dasan.rst11 overruns in C/C++ programs, and other similar errors, as well as
31 - The libasan package must be installed when compiling with gcc in Centos/RHEL.
42 Add below unit test code in examples/helloworld/main.c::
55 #0 0x5652e6707b83 in main ../examples/helloworld/main.c:47
56 #1 0x7fb94953c0b2 in __libc_start_main (/lib/x86_64-linux-gnu/libc.so.6+0x270b2)
57 …#2 0x5652e67079bd in _start (/home/pzh/asan_test/x86_64-native-linuxapp-gcc/examples/dpdk-hellowor…
60 SUMMARY: AddressSanitizer: heap-buffer-overflow ../examples/helloworld/main.c:47 in main
70 Add below unit test code in examples/helloworld/main.c::
84 #0 0x564308a39b88 in main ../examples/helloworld/main.c:48
85 #1 0x7fd0079c60b2 in __libc_start_main (/lib/x86_64-linux-gnu/libc.so.6+0x270b2)
[all …]
/dpdk/examples/ipsec-secgw/
H A Dep0.cfg25 sp ipv4 in esp protect 105 pri 1 dst 192.168.115.0/24 sport 0:65535 dport 0:65535
26 sp ipv4 in esp protect 106 pri 1 dst 192.168.116.0/24 sport 0:65535 dport 0:65535
27 sp ipv4 in esp protect 110 pri 1 dst 192.168.185.0/24 sport 0:65535 dport 0:65535
33 sp ipv4 in esp protect 125 pri 1 dst 192.168.65.0/24 sport 0:65535 dport 0:65535
34 sp ipv4 in esp protect 125 pri 1 dst 192.168.65.0/24 sport 0:65535 dport 0:65535
35 sp ipv4 in esp protect 126 pri 1 dst 192.168.66.0/24 sport 0:65535 dport 0:65535
36 sp ipv4 in esp bypass pri 1 dst 192.168.245.0/24 sport 0:65535 dport 0:65535
37 sp ipv4 in esp bypass pri 1 dst 192.168.246.0/24 sport 0:65535 dport 0:65535
119 sa in 115 cipher_algo null auth_algo null mode ipv4-tunnel src 172.16.2.5 \
124 sa in 117 cipher_algo null auth_algo null mode ipv4-tunnel src 172.16.2.7 \
[all …]
/dpdk/lib/eal/include/generic/
H A Drte_pflock.h42 uint16_t in; member
93 pf->rd.in = 0; in rte_pflock_init()
95 pf->wr.in = 0; in rte_pflock_init()
118 w = __atomic_fetch_add(&pf->rd.in, RTE_PFLOCK_RINC, __ATOMIC_ACQUIRE) in rte_pflock_read_lock()
124 RTE_WAIT_UNTIL_MASKED(&pf->rd.in, RTE_PFLOCK_WBITS, !=, w, in rte_pflock_read_lock()
162 ticket = __atomic_fetch_add(&pf->wr.in, 1, __ATOMIC_RELAXED); in rte_pflock_write_lock()
174 ticket = __atomic_fetch_add(&pf->rd.in, w, __ATOMIC_RELAXED); in rte_pflock_write_lock()
194 __atomic_fetch_and(&pf->rd.in, RTE_PFLOCK_LSB, __ATOMIC_RELEASE); in rte_pflock_write_unlock()
/dpdk/drivers/net/sfc/
H A Dsfc_flow_rss.c82 if (in->level) { in sfc_flow_rss_parse_conf()
92 if (in->types != 0) { in sfc_flow_rss_parse_conf()
104 if (in->key_len != 0) { in sfc_flow_rss_parse_conf()
111 if (in->key == NULL) { in sfc_flow_rss_parse_conf()
116 key = in->key; in sfc_flow_rss_parse_conf()
124 switch (in->func) { in sfc_flow_rss_parse_conf()
143 out->rte_hash_function = in->func; in sfc_flow_rss_parse_conf()
145 if (in->queue_num == 0) { in sfc_flow_rss_parse_conf()
156 if (in->queue == NULL) { in sfc_flow_rss_parse_conf()
167 uint16_t sw_qid = in->queue[i]; in sfc_flow_rss_parse_conf()
[all …]
/dpdk/doc/guides/howto/
H A Ddebug_troubleshoot.rst38 The overview of an application modeled using PMD is shown in
58 Is there mismatch in packet (received < desired) rate?
189 Is there a variance in packet or object processing rate in the pipeline?
213 * Packet buffer copy in fast path also results in stalls in MBUF release if
244 Is there a variance in cryptodev performance?
354 Is there a bottleneck in the performance of eventdev?
367 #. If there are performance drops in the enqueue stage
376 Is there a variance in traffic manager?
394 #. Isolate the flow in which the undesired drops occur. Use
402 Is the packet in the unexpected format?
[all …]

12345678910>>...22