Home
last modified time | relevance | path

Searched refs:pos (Results 1 – 25 of 143) sorted by relevance

123456

/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_sse.h44 unsigned int pos; in rxq_copy_mbuf_v() local
47 for (pos = 0; pos < p; pos += 2) { in rxq_copy_mbuf_v()
54 pkts[pos] = elts[pos]; in rxq_copy_mbuf_v()
78 unsigned int pos; in rxq_cq_decompress_v() local
127 for (pos = 0; pos < mcqe_n; ) { in rxq_cq_decompress_v()
347 if (!(pos & 0x7) && pos < mcqe_n) { in rxq_cq_decompress_v()
586 for (pos = 0; in rxq_cq_process_v()
740 pkts[pos]->port = cq[pos].user_index_low; in rxq_cq_process_v()
741 pkts[pos + p1]->port = cq[pos + p1].user_index_low; in rxq_cq_process_v()
742 pkts[pos + p2]->port = cq[pos + p2].user_index_low; in rxq_cq_process_v()
[all …]
H A Dmlx5_rxtx_vec_neon.h42 unsigned int pos; in rxq_copy_mbuf_v() local
45 for (pos = 0; pos < p; pos += 2) { in rxq_copy_mbuf_v()
52 pkts[pos] = elts[pos]; in rxq_copy_mbuf_v()
76 unsigned int pos; in rxq_cq_decompress_v() local
134 for (pos = 0; pos < mcqe_n; ) { in rxq_cq_decompress_v()
271 mcq[pos % 8].hdr_type; in rxq_cq_decompress_v()
357 if (!(pos & 0x7) && pos < mcqe_n) { in rxq_cq_decompress_v()
358 if (pos + 8 < mcqe_n) in rxq_cq_decompress_v()
527 unsigned int pos; in rxq_cq_process_v() local
614 for (pos = 0; in rxq_cq_process_v()
[all …]
H A Dmlx5_rxtx_vec_altivec.h46 unsigned int pos; in rxq_copy_mbuf_v() local
49 for (pos = 0; pos < p; pos += 2) { in rxq_copy_mbuf_v()
57 pkts[pos] = elts[pos]; in rxq_copy_mbuf_v()
113 unsigned int pos; in rxq_cq_decompress_v() local
135 for (pos = 0; pos < mcqe_n; ) { in rxq_cq_decompress_v()
491 if (!(pos & 0x7) && pos < mcqe_n) { in rxq_cq_decompress_v()
861 for (pos = 0; in rxq_cq_process_v()
1193 pkts[pos]->port = cq[pos].user_index_low; in rxq_cq_process_v()
1194 pkts[pos + p1]->port = cq[pos + p1].user_index_low; in rxq_cq_process_v()
1195 pkts[pos + p2]->port = cq[pos + p2].user_index_low; in rxq_cq_process_v()
[all …]
/dpdk/app/test/
H A Dtest_hash.c526 RETURN_IF_ERROR(pos < 0, "failed to add key (pos=%d)", pos); in test_add_delete_free_lf()
533 delPos = pos; in test_add_delete_free_lf()
569 delPos = pos; in test_add_delete_free_lf()
708 int pos[5]; in test_five_keys() local
805 int pos[5]; in test_full_bucket() local
909 int pos[64]; in test_extendable_bucket() local
1982 pos[i]); in test_hash_rcu_qsbr_dq_mode()
1997 pos[0]); in test_hash_rcu_qsbr_dq_mode()
2004 pos[0]); in test_hash_rcu_qsbr_dq_mode()
2036 pos[0]); in test_hash_rcu_qsbr_dq_mode()
[all …]
H A Dtest_bitmap.c21 uint32_t pos = 0, start_pos; in test_bitmap_scan_operations() local
27 rte_bitmap_set_slab(bmp, pos, slab1_magic); in test_bitmap_scan_operations()
30 if (!rte_bitmap_scan(bmp, &pos, &out_slab)) { in test_bitmap_scan_operations()
91 start_pos = pos; in test_bitmap_scan_operations()
97 } while (pos != start_pos); in test_bitmap_scan_operations()
111 uint32_t pos = 0; in test_bitmap_slab_set_get() local
116 rte_bitmap_set_slab(bmp, pos, slab_magic); in test_bitmap_slab_set_get()
223 uint32_t pos; in test_bitmap_all_set() local
243 pos = slab = 0; in test_bitmap_all_set()
249 rte_bitmap_clear(bmp, pos); in test_bitmap_all_set()
[all …]
/dpdk/drivers/common/sfc_efx/base/
H A Defx_vpd.c424 keyword = EFX_VPD_KEYWORD(tag[pos], tag[pos + 1]); in efx_vpd_next_keyword()
486 unsigned int pos; in efx_vpd_hunk_verify() local
509 for (pos = 0; pos != taglen; pos += 3 + keylen) { in efx_vpd_hunk_verify()
585 unsigned int pos; in efx_vpd_hunk_reinit() local
606 for (pos = 0; pos < offset; pos++) in efx_vpd_hunk_reinit()
639 unsigned int pos; in efx_vpd_hunk_next() local
669 for (pos = 0; pos != taglen; pos += 3 + keylen) { in efx_vpd_hunk_next()
740 for (pos = 0; pos != taglen; pos += 3 + keylen) { in efx_vpd_hunk_get()
842 pos = 0; in efx_vpd_hunk_set()
851 for (pos = 0; pos != taglen; pos += 3 + keylen) { in efx_vpd_hunk_set()
[all …]
H A Def10_mcdi.c143 unsigned int pos; in ef10_mcdi_send_request() local
148 for (pos = 0; pos < hdr_len; pos += sizeof (efx_dword_t)) { in ef10_mcdi_send_request()
149 dword = *(efx_dword_t *)((uint8_t *)hdrp + pos); in ef10_mcdi_send_request()
150 EFSYS_MEM_WRITED(esmp, pos, &dword); in ef10_mcdi_send_request()
154 for (pos = 0; pos < sdu_len; pos += sizeof (efx_dword_t)) { in ef10_mcdi_send_request()
155 dword = *(efx_dword_t *)((uint8_t *)sdup + pos); in ef10_mcdi_send_request()
156 EFSYS_MEM_WRITED(esmp, hdr_len + pos, &dword); in ef10_mcdi_send_request()
214 unsigned int pos = 0; in ef10_mcdi_read_response() local
221 EFSYS_MEM_READD(esmp, offset + pos, &data); in ef10_mcdi_read_response()
222 memcpy((uint8_t *)bufferp + pos, &data, chunk); in ef10_mcdi_read_response()
[all …]
H A Dsiena_mcdi.c40 unsigned int pos; in siena_mcdi_send_request() local
54 for (pos = 0; pos < sdu_len; pos += sizeof (efx_dword_t)) { in siena_mcdi_send_request()
55 dword = *(efx_dword_t *)((uint8_t *)sdup + pos); in siena_mcdi_send_request()
57 pdur + 1 + (pos >> 2), &dword, B_FALSE); in siena_mcdi_send_request()
127 unsigned int pos = 0; in siena_mcdi_read_response() local
138 pdur + ((offset + pos) >> 2), &data, B_FALSE); in siena_mcdi_read_response()
139 memcpy((uint8_t *)bufferp + pos, &data, chunk); in siena_mcdi_read_response()
140 pos += chunk; in siena_mcdi_read_response()
/dpdk/lib/table/
H A Drte_lru.h48 uint64_t x, pos, x0, x1, x2, mask; \
52 pos = 4; \
54 pos = 3; \
57 pos = 2; \
60 pos = 1; \
63 pos = 0; \
66 pos <<= 4; \
67 mask = (~0LLU) << pos; \
70 x2 = (x << (48 - pos)) & (0xFFFFLLU << 48); \
73 if (pos != 64) \
H A Drte_table_hash_cuckoo.c158 int pos = 0; in rte_table_hash_cuckoo_entry_add() local
170 if (pos >= 0) { in rte_table_hash_cuckoo_entry_add()
181 if (pos == -ENOENT) { in rte_table_hash_cuckoo_entry_add()
186 if (pos < 0) in rte_table_hash_cuckoo_entry_add()
187 return pos; in rte_table_hash_cuckoo_entry_add()
197 return pos; in rte_table_hash_cuckoo_entry_add()
205 int pos = 0; in rte_table_hash_cuckoo_entry_delete() local
214 if (pos >= 0) { in rte_table_hash_cuckoo_entry_delete()
226 return pos; in rte_table_hash_cuckoo_entry_delete()
278 int pos; in rte_table_hash_cuckoo_lookup() local
[all …]
/dpdk/lib/eal/include/
H A Drte_bitmap.h221 uint32_t pos) in __rte_bitmap_clear_slab_overhead_bits() argument
339 index2 = pos >> RTE_BITMAP_SLAB_BIT_SIZE_LOG2; in rte_bitmap_prefetch0()
360 index2 = pos >> RTE_BITMAP_SLAB_BIT_SIZE_LOG2; in rte_bitmap_get()
361 offset2 = pos & RTE_BITMAP_SLAB_BIT_MASK; in rte_bitmap_get()
381 index2 = pos >> RTE_BITMAP_SLAB_BIT_SIZE_LOG2; in rte_bitmap_set()
382 offset2 = pos & RTE_BITMAP_SLAB_BIT_MASK; in rte_bitmap_set()
409 index2 = pos >> RTE_BITMAP_SLAB_BIT_SIZE_LOG2; in rte_bitmap_set_slab()
474 index2 = pos >> RTE_BITMAP_SLAB_BIT_SIZE_LOG2; in rte_bitmap_clear()
475 offset2 = pos & RTE_BITMAP_SLAB_BIT_MASK; in rte_bitmap_clear()
580 if (__rte_bitmap_scan_read(bmp, pos, slab)) { in rte_bitmap_scan()
[all …]
/dpdk/lib/ring/
H A Drte_ring_hts_elem_pvt.h33 __atomic_store_n(&ht->ht.pos.tail, tail, __ATOMIC_RELEASE); in __rte_ring_hts_update_tail()
45 while (p->pos.head != p->pos.tail) { in __rte_ring_hts_head_wait()
83 *free_entries = capacity + r->cons.tail - op.pos.head; in __rte_ring_hts_move_prod_head()
93 np.pos.tail = op.pos.tail; in __rte_ring_hts_move_prod_head()
94 np.pos.head = op.pos.head + n; in __rte_ring_hts_move_prod_head()
105 *old_head = op.pos.head; in __rte_ring_hts_move_prod_head()
139 *entries = r->prod.tail - op.pos.head; in __rte_ring_hts_move_cons_head()
148 np.pos.tail = op.pos.tail; in __rte_ring_hts_move_cons_head()
149 np.pos.head = op.pos.head + n; in __rte_ring_hts_move_cons_head()
160 *old_head = op.pos.head; in __rte_ring_hts_move_cons_head()
H A Drte_ring_rts_elem_pvt.h42 nt.val.pos = h.val.pos; in __rte_ring_rts_update_tail()
60 while (h->val.pos - ht->tail.val.pos > max) { in __rte_ring_rts_head_wait()
98 *free_entries = capacity + r->cons.tail - oh.val.pos; in __rte_ring_rts_move_prod_head()
108 nh.val.pos = oh.val.pos + n; in __rte_ring_rts_move_prod_head()
120 *old_head = oh.val.pos; in __rte_ring_rts_move_prod_head()
154 *entries = r->prod.tail - oh.val.pos; in __rte_ring_rts_move_cons_head()
163 nh.val.pos = oh.val.pos + n; in __rte_ring_rts_move_cons_head()
175 *old_head = oh.val.pos; in __rte_ring_rts_move_cons_head()
H A Drte_ring_peek_elem_pvt.h56 uint32_t pos; in __rte_ring_st_set_head_tail() local
60 pos = tail + num; in __rte_ring_st_set_head_tail()
61 ht->head = pos; in __rte_ring_st_set_head_tail()
62 __atomic_store_n(&ht->tail, pos, __ATOMIC_RELEASE); in __rte_ring_st_set_head_tail()
82 n = p.pos.head - p.pos.tail; in __rte_ring_hts_get_tail()
87 *tail = p.pos.tail; in __rte_ring_hts_get_tail()
104 p.pos.head = tail + num; in __rte_ring_hts_set_head_tail()
105 p.pos.tail = p.pos.head; in __rte_ring_hts_set_head_tail()
/dpdk/drivers/net/hns3/
H A Dhns3_rxtx_vec_neon.h139 uint32_t pos; in hns3_recv_burst_vec() local
167 for (pos = 0; pos < nb_pkts; pos += HNS3_DEFAULT_DESCS_PER_LOOP, in hns3_recv_burst_vec()
184 mbp1 = vld1q_u64((uint64_t *)&sw_ring[pos]); in hns3_recv_burst_vec()
194 mbp2 = vld1q_u64((uint64_t *)&sw_ring[pos + 2]); in hns3_recv_burst_vec()
207 vst1q_u64((uint64_t *)&rx_pkts[pos], mbp1); in hns3_recv_burst_vec()
214 vst1q_u64((uint64_t *)&rx_pkts[pos + 2], mbp2); in hns3_recv_burst_vec()
230 *(uint64_t *)&sw_ring[pos + 0].mbuf->rearm_data = in hns3_recv_burst_vec()
281 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
283 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
285 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
[all …]
/dpdk/drivers/net/nfp/
H A Dnfp_cpp_bridge.c59 uint32_t cpp_id, pos, len; in nfp_cpp_bridge_serve_write() local
112 for (pos = 0; pos < curlen; pos += len) { in nfp_cpp_bridge_serve_write()
113 len = curlen - pos; in nfp_cpp_bridge_serve_write()
128 err = nfp_cpp_area_write(area, pos, tmpbuf, len); in nfp_cpp_bridge_serve_write()
137 nfp_offset += pos; in nfp_cpp_bridge_serve_write()
141 count -= pos; in nfp_cpp_bridge_serve_write()
160 uint32_t cpp_id, pos, len; in nfp_cpp_bridge_serve_read() local
211 for (pos = 0; pos < curlen; pos += len) { in nfp_cpp_bridge_serve_read()
212 len = curlen - pos; in nfp_cpp_bridge_serve_read()
237 nfp_offset += pos; in nfp_cpp_bridge_serve_read()
[all …]
/dpdk/drivers/crypto/scheduler/
H A Dscheduler_pkt_size_distr.c33 uint16_t pos; member
83 if (p_enq_op->pos + in_flight_ops[p_enq_op->worker_idx] == in schedule_enqueue()
89 sched_ops[p_enq_op->worker_idx][p_enq_op->pos] = ops[i]; in schedule_enqueue()
90 p_enq_op->pos++; in schedule_enqueue()
104 p_enq_op->pos++; in schedule_enqueue()
118 p_enq_op->pos++; in schedule_enqueue()
132 p_enq_op->pos++; in schedule_enqueue()
147 sched_ops[p_enq_op->worker_idx][p_enq_op->pos] = ops[i]; in schedule_enqueue()
148 p_enq_op->pos++; in schedule_enqueue()
155 enq_ops[PRIMARY_WORKER_IDX].pos); in schedule_enqueue()
[all …]
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c205 int pos; in _recv_raw_pkts_vec() local
274 for (pos = 0, nb_pkts_recd = 0; pos < nb_pkts; in _recv_raw_pkts_vec()
275 pos += RTE_I40E_DESCS_PER_LOOP, in _recv_raw_pkts_vec()
308 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
309 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
310 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _recv_raw_pkts_vec()
413 rx_pkts[pos]->next = NULL; in _recv_raw_pkts_vec()
414 rx_pkts[pos + 1]->next = NULL; in _recv_raw_pkts_vec()
415 rx_pkts[pos + 2]->next = NULL; in _recv_raw_pkts_vec()
416 rx_pkts[pos + 3]->next = NULL; in _recv_raw_pkts_vec()
[all …]
H A Di40e_rxtx_vec_neon.c342 int pos; in _recv_raw_pkts_vec() local
407 for (pos = 0, nb_pkts_recd = 0; pos < nb_pkts; in _recv_raw_pkts_vec()
408 pos += RTE_I40E_DESCS_PER_LOOP, in _recv_raw_pkts_vec()
439 vst1q_u64((uint64_t *)&rx_pkts[pos], mbp1); in _recv_raw_pkts_vec()
443 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
444 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
445 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _recv_raw_pkts_vec()
544 rx_pkts[pos]->next = NULL; in _recv_raw_pkts_vec()
545 rx_pkts[pos + 1]->next = NULL; in _recv_raw_pkts_vec()
546 rx_pkts[pos + 2]->next = NULL; in _recv_raw_pkts_vec()
[all …]
/dpdk/drivers/net/ice/base/
H A Dice_osdep.h364 #define LIST_FOR_EACH_ENTRY(pos, head, type, member) \ argument
365 for ((pos) = (head)->lh_first ? \
368 (pos); \
369 (pos) = (pos)->member.next.le_next ? \
370 container_of((pos)->member.next.le_next, struct type, \
375 for ((pos) = (head)->lh_first ? \
378 (tmp) = (pos) == 0 ? 0 : ((pos)->member.next.le_next ? \
382 (pos); \
383 (pos) = (tmp), \
400 #define HLIST_FOR_EACH_ENTRY(pos, head, type, member) \ argument
[all …]
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_sse.c398 int pos; in _recv_raw_pkts_vec() local
484 for (pos = 0, nb_pkts_recd = 0; pos < nb_pkts; in _recv_raw_pkts_vec()
485 pos += IAVF_VPMD_DESCS_PER_LOOP, in _recv_raw_pkts_vec()
524 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
525 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
526 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _recv_raw_pkts_vec()
527 rte_mbuf_prefetch_part2(rx_pkts[pos + 3]); in _recv_raw_pkts_vec()
647 int pos; in _recv_raw_pkts_vec_flex_rxd() local
747 for (pos = 0, nb_pkts_recd = 0; pos < nb_pkts; in _recv_raw_pkts_vec_flex_rxd()
748 pos += IAVF_VPMD_DESCS_PER_LOOP, in _recv_raw_pkts_vec_flex_rxd()
[all …]
/dpdk/drivers/raw/ifpga/
H A Difpga_rawdev.h34 #define IFPGA_BIT_SET(var, pos) \ argument
35 ((var) |= ((uint64_t)1 << ((pos))))
38 #define IFPGA_BIT_RESET(var, pos) \ argument
39 ((var) &= ~((uint64_t)1 << ((pos))))
42 #define IFPGA_BIT_ISSET(var, pos) \ argument
43 (((var) & ((uint64_t)1 << ((pos)))) ? 1 : 0)
/dpdk/lib/ethdev/
H A Dethdev_private.c78 char *pos = str; in rte_eth_devargs_process_range() local
94 return pos + n; in rte_eth_devargs_process_range()
109 char *pos = str; in rte_eth_devargs_process_list() local
111 if (*pos == '[') in rte_eth_devargs_process_list()
112 pos++; in rte_eth_devargs_process_list()
114 pos = rte_eth_devargs_process_range(pos, list, len_list, in rte_eth_devargs_process_list()
116 if (pos == NULL) in rte_eth_devargs_process_list()
120 pos++; in rte_eth_devargs_process_list()
124 if (*pos == ']') in rte_eth_devargs_process_list()
125 pos++; in rte_eth_devargs_process_list()
[all …]
/dpdk/drivers/net/virtio/
H A Dvirtio_pci.c57 uint8_t pos; in vtpci_msix_detect() local
67 while (pos) { in vtpci_msix_detect()
74 pos, ret); in vtpci_msix_detect()
82 pos + sizeof(cap)); in vtpci_msix_detect()
96 pos = cap[1]; in vtpci_msix_detect()
638 uint8_t pos; in virtio_read_caps() local
654 while (pos) { in virtio_read_caps()
659 pos, ret); in virtio_read_caps()
672 pos + 2); in virtio_read_caps()
697 pos, ret); in virtio_read_caps()
[all …]
/dpdk/drivers/common/dpaax/caamflib/rta/
H A Dload_cmd.h147 load_check_len_offset(int pos, uint32_t length, uint32_t offset) in load_check_len_offset() argument
149 if ((load_dst[pos].dst == DCTRL) && in load_check_len_offset()
154 switch (load_dst[pos].len_off) { in load_check_len_offset()
219 int pos = -1, ret = -EINVAL; in rta_load() local
240 pos = (int)i; in rta_load()
243 if (-1 == pos) { in rta_load()
250 if (load_dst[pos].imm_src == IMM_NO) { in rta_load()
256 } else if (load_dst[pos].imm_src == IMM_MUST) { in rta_load()
262 ret = load_check_len_offset(pos, length, offset); in rta_load()
269 opcode |= load_dst[pos].dst_opcode; in rta_load()

123456