Home
last modified time | relevance | path

Searched refs:first (Results 1 – 25 of 183) sorted by relevance

12345678

/dpdk/lib/cmdline/
H A Dcmdline_parse_portlist.c35 const char *first, *last; in parse_ports() local
38 for (first = str, last = first; in parse_ports()
39 first != NULL && last != NULL; in parse_ports()
40 first = last + 1) { in parse_ports()
42 last = strchr(first, ','); in parse_ports()
45 ps = strtoul(first, &end, 10); in parse_ports()
46 if (errno != 0 || end == first || in parse_ports()
53 first = end + 1; in parse_ports()
54 pe = strtoul(first, &end, 10); in parse_ports()
55 if (errno != 0 || end == first || in parse_ports()
/dpdk/lib/stack/
H A Drte_stack_lf.h40 struct rte_stack_lf_elem *tmp, *first, *last = NULL; in __rte_stack_lf_push() local
47 first = __rte_stack_lf_pop_elems(&s->stack_lf.free, n, NULL, &last); in __rte_stack_lf_push()
48 if (unlikely(first == NULL)) in __rte_stack_lf_push()
52 for (tmp = first, i = 0; i < n; i++, tmp = tmp->next) in __rte_stack_lf_push()
56 __rte_stack_lf_push_elems(&s->stack_lf.used, first, last, n); in __rte_stack_lf_push()
76 struct rte_stack_lf_elem *first, *last = NULL; in __rte_stack_lf_pop() local
82 first = __rte_stack_lf_pop_elems(&s->stack_lf.used, in __rte_stack_lf_pop()
84 if (unlikely(first == NULL)) in __rte_stack_lf_pop()
88 __rte_stack_lf_push_elems(&s->stack_lf.free, first, last, n); in __rte_stack_lf_pop()
H A Drte_stack_lf_stubs.h20 struct rte_stack_lf_elem *first, in __rte_stack_lf_push_elems() argument
24 RTE_SET_USED(first); in __rte_stack_lf_push_elems()
H A Drte_stack_lf_c11.h35 struct rte_stack_lf_elem *first, in __rte_stack_lf_push_elems() argument
50 new_head.top = first; in __rte_stack_lf_push_elems()
H A Drte_stack_lf_generic.h35 struct rte_stack_lf_elem *first, in __rte_stack_lf_push_elems() argument
57 new_head.top = first; in __rte_stack_lf_push_elems()
/dpdk/drivers/net/mlx5/windows/
H A Dmlx5_flow_os.c254 static struct mlx5_workspace_thread *first; variable
284 struct mlx5_workspace_thread *temp = first; in mlx5_clear_thread_list()
299 if (temp == first) { in mlx5_clear_thread_list()
302 first = temp->next; in mlx5_clear_thread_list()
327 if (first) { in mlx5_flow_os_release_workspace()
328 MLX5_ASSERT(!first->next); in mlx5_flow_os_release_workspace()
329 flow_release_workspace(first->mlx5_ws); in mlx5_flow_os_release_workspace()
330 free(first); in mlx5_flow_os_release_workspace()
357 if (!first) { in mlx5_add_workspace_to_list()
358 first = temp; in mlx5_add_workspace_to_list()
/dpdk/app/test/
H A Dtest_fbarray.c467 int len = last - first + 1; in test_biggest()
470 TEST_ASSERT((first == -1) == (last == -1), in test_biggest()
474 if (first == -1) { in test_biggest()
483 } else if (first == 0) { in test_biggest()
490 lo_free_space_last = first - 1; in test_biggest()
530 TEST_ASSERT_EQUAL(rte_fbarray_find_biggest_used(arr, 0), first, in test_biggest()
533 first, in test_biggest()
592 if (first != -1) { in test_biggest()
593 TEST_ASSERT_EQUAL(rte_fbarray_find_biggest_free(arr, first), in test_biggest()
616 int i, len = last - first + 1; in ensure_correct()
[all …]
/dpdk/lib/eal/common/
H A Deal_common_fbarray.c129 first = MASK_LEN_TO_IDX(start); in find_next_n()
277 first = MASK_LEN_TO_IDX(start); in find_next()
300 if (idx == first) in find_next()
336 first = MASK_LEN_TO_IDX(start); in find_contig()
353 if (idx == first) { in find_contig()
394 first = MASK_LEN_TO_IDX(start); in find_prev_n()
402 msk_idx = first; in find_prev_n()
564 idx = first; in find_prev()
574 if (idx == first) in find_prev()
609 idx = first; in find_rev_contig()
[all …]
H A Dmalloc_elem.c150 if ((heap->first == NULL) != (heap->last == NULL)) { in malloc_elem_insert()
155 if (heap->first == NULL && heap->last == NULL) { in malloc_elem_insert()
157 heap->first = elem; in malloc_elem_insert()
161 } else if (elem < heap->first) { in malloc_elem_insert()
164 next_elem = heap->first; in malloc_elem_insert()
165 heap->first = elem; in malloc_elem_insert()
176 dist_from_start = RTE_PTR_DIFF(elem, heap->first); in malloc_elem_insert()
180 prev_elem = heap->first; in malloc_elem_insert()
332 elem->heap->first = next; in remove_elem()
/dpdk/drivers/bus/fslmc/qbman/
H A Dqbman_portal.h30 static inline uint8_t qm_cyc_diff(uint8_t ringsize, uint8_t first, in qm_cyc_diff() argument
34 if (first <= last) in qm_cyc_diff()
35 return last - first; in qm_cyc_diff()
36 return (2 * ringsize) + last - first; in qm_cyc_diff()
/dpdk/examples/vdpa/
H A Dmain.c393 uint32_t first, last; in cmd_device_stats_parsed() local
412 first = 0; in cmd_device_stats_parsed()
421 first = res->qid; in cmd_device_stats_parsed()
450 for (; first <= last; first++) { in cmd_device_stats_parsed()
452 if (rte_vdpa_get_stats(vport->dev, (int)first, vport->stats, in cmd_device_stats_parsed()
456 (int)first); in cmd_device_stats_parsed()
459 cmdline_printf(cl, "\tVirtq %" PRIu32 ":\n", first); in cmd_device_stats_parsed()
/dpdk/doc/guides/
H A Dcustom.css8 * Complex list items start with a p.first element. */
9 .section li > .first {
/dpdk/doc/guides/prog_guide/
H A Dlpm_lib.rst56 The first table, called tbl24, is indexed using the first 24 bits of the IP address to be looked up,
84 The first field can either contain a number indicating the tbl8 in which the lookup process should …
127 * Use the first 24 bits of the rule as an index to the tbl24.
138 This means that there are 2^(24 - 20) = 16 different combinations of the first 24 bits of an IP add…
185 * Use the first 24 bits of the IP address as an index to the tbl24.
199 The first one is the maximum number of rules, which is a parameter passed through the API.
210 and the first 24 bits of this rule are not the same as the first 24 bits of a rule previously added.
214 …lue of 256, we can have up to 256 rules longer than 24 bits that differ on their first three bytes.
H A Dlpm6_lib.rst71 The first table, called tbl24, is indexed using the first 24 bits of the IP address be looked up,
102 The first field can either contain a number indicating the tbl8 in which the lookup process should …
134 * Use the first 24 bits of the rule as an index to the tbl24.
151 This means that there are 2^(24-20) = 16 different combinations of the first 24 bits of an IP addre…
167 * Use the first 24 bits of the IP address as an index to the tbl24.
183 The first one is the maximum number of rules, which is a parameter passed through the API.
191 which is the number of levels minus one, since the first three bytes are resolved in the tbl24. How…
196 depending on what their first bytes are.
197 If they share the same first 24 bits, for instance, the tbl8 at the second level will be shared.
/dpdk/drivers/net/qede/base/
H A Decore_cxt.c341 p_cli->first.val = *p_line; in ecore_ilt_cli_adv_line()
350 client_id, p_cli->first.val, p_cli->last.val, in ecore_ilt_cli_adv_line()
384 p_cli->first.val = 0; in ecore_cxt_set_cli()
482 p_cli->first.val = curr_line; in ecore_cxt_cfg_ilt_compute()
539 p_cli->pf_total_lines = curr_line - p_cli->first.val; in ecore_cxt_cfg_ilt_compute()
834 ilt_clients[i].first.val + 1); in ecore_cxt_ilt_shadow_size()
1386 p_cli->first.val)) / CDUT_SEG_ALIGNMET_IN_BYTES; in ecore_cdu_init_pf()
1395 p_cli->first.val)) / CDUT_SEG_ALIGNMET_IN_BYTES; in ecore_cdu_init_pf()
1496 ilt_clients[i].first.reg, in ecore_ilt_bounds_init()
1497 ilt_clients[i].first.val); in ecore_ilt_bounds_init()
[all …]
/dpdk/lib/fib/
H A Dtrie_avx512.c13 __m512i *first, __m512i *second, __m512i *third, __m512i *fourth) in transpose_x16() argument
41 *first = _mm512_permutexvar_epi32(perm_idxes.z, tmp1); in transpose_x16()
52 __m512i *first, __m512i *second) in transpose_x8() argument
64 *first = _mm512_permutexvar_epi64(perm_idxes.z, tmp3); in transpose_x8()
/dpdk/doc/guides/cryptodevs/
H A Dmlx5.rst39 (Key Encrypting Key) should be set as the first step.
52 Operational, while setting the first import_KEK and credential in plaintext.
59 - The first credential in plaintext, 40B.
60 - The first import_KEK in plaintext: kek size 0 for 16B or 1 for 32B, kek data.
/dpdk/doc/guides/sample_app_ug/
H A Dipv4_multicast.rst29 The max port mask supported in the given hash table is 0xf, so only first
189 The first approach creates a clone of the input packet, for example,
198 Basically, the first approach reuses only the input packet's data, but creates its own copy of pack…
201 The advantage of first approach is that each outgoing packet has its own copy of the metadata,
214 first approach is faster.
218 either the first (with cloning) or the second (without cloning) approach is taken:
/dpdk/drivers/raw/ifpga/base/
H A Difpga_feature_dev.c134 struct feature_port_first_err_key first; in port_err_clear() local
176 first.csr = readq(&port_err->port_first_error); in port_err_clear()
177 writeq(first.csr, &port_err->port_first_error); in port_err_clear()
/dpdk/license/
H A DREADME20 DPDK uses first line of the file to be SPDX tag. In case of *#!* scripts, SPDX
53 first listed.
55 advise the author to check alternate means first. If no other alternative
/dpdk/examples/pipeline/examples/
H A Dvarbit.spec6 ; the start of the UDP header, the size of the IPv4 header needs to be detected first, which is done
7 ; by reading the first byte of the IPv4 header that carries the 4-bit Internet Header Length (IHL)
/dpdk/drivers/bus/dpaa/base/qbman/
H A Dbman.h67 static inline u8 bm_cyc_diff(u8 ringsize, u8 first, u8 last) in bm_cyc_diff() argument
70 if (first <= last) in bm_cyc_diff()
71 return last - first; in bm_cyc_diff()
72 return ringsize + last - first; in bm_cyc_diff()
/dpdk/lib/pipeline/
H A Drte_swx_ctl.c212 first = &table->mf[0]; in table_params_get()
218 if (f->offset < first->offset) in table_params_get()
219 first = f; in table_params_get()
237 key_offset = first->offset / 8; in table_params_get()
251 start = (f->offset - first->offset) / 8; in table_params_get()
275 table->mf_first = first; in table_params_get()
910 first = &s->selector_fields[0]; in selector_params_get()
916 if (f->offset < first->offset) in selector_params_get()
917 first = f; in selector_params_get()
924 selector_offset = first->offset / 8; in selector_params_get()
[all …]
/dpdk/lib/eal/include/
H A Drte_trace_point_register.h13 #error for registration, include this file first before <rte_trace_point.h>
/dpdk/doc/guides/mempool/
H A Dcnxk.rst62 provide ``max_pools`` parameter to the first PCIe device probed by the given
84 driver configures an NPA LF and attach to the first probed ethdev or eventdev

12345678