| /dpdk/drivers/gpu/cuda/ |
| H A D | cuda.c | 338 CUresult res; in cuda_pfn_func_loader() local
342 if (res != 0) { in cuda_pfn_func_loader()
349 if (res != 0) { in cuda_pfn_func_loader()
356 if (res != 0) { in cuda_pfn_func_loader()
591 CUresult res; in cuda_dev_info_get() local
708 CUresult res; in cuda_mem_alloc() local
801 CUresult res; in cuda_mem_register() local
965 CUresult res; in cuda_mem_unregister() local
1039 CUresult res; in cuda_mem_free() local
1095 CUresult res; in cuda_wmb() local
[all …]
|
| /dpdk/drivers/net/nfp/nfpcore/ |
| H A D | nfp_resource.c | 99 res->mutex = in nfp_cpp_resource_find()
160 res = malloc(sizeof(*res)); in nfp_resource_acquire()
161 if (!res) in nfp_resource_acquire()
164 memset(res, 0, sizeof(*res)); in nfp_resource_acquire()
172 free(res); in nfp_resource_acquire()
198 return res; in nfp_resource_acquire()
202 free(res); in nfp_resource_acquire()
217 free(res); in nfp_resource_release()
241 return res->name; in nfp_resource_name()
253 return res->addr; in nfp_resource_address()
[all …]
|
| /dpdk/drivers/net/octeontx/base/ |
| H A D | octeontx_bgx.c | 15 int res; in octeontx_bgx_port_open() local
23 if (res < 0) in octeontx_bgx_port_open()
39 return res; in octeontx_bgx_port_open()
46 int res; in octeontx_bgx_port_close() local
63 int res; in octeontx_bgx_port_start() local
80 int res; in octeontx_bgx_port_stop() local
99 int res; in octeontx_bgx_port_get_config() local
132 int res; in octeontx_bgx_port_status() local
153 int res; in octeontx_bgx_port_stats() local
178 int res; in octeontx_bgx_port_stats_clr() local
[all …]
|
| H A D | octeontx_pkivf.c | 34 int i, res; in octeontx_pki_port_open() local
53 if (res < 0) in octeontx_pki_port_open()
55 return res; in octeontx_pki_port_open()
62 int res; in octeontx_pki_port_hash_config() local
75 return res; in octeontx_pki_port_hash_config()
82 int res; in octeontx_pki_port_pktbuf_config() local
94 return res; in octeontx_pki_port_pktbuf_config()
101 int res; in octeontx_pki_port_create_qos() local
122 int res; in octeontx_pki_port_errchk_config() local
144 int res; in octeontx_pki_port_vlan_fltr_config() local
[all …]
|
| H A D | octeontx_pkovf.c | 131 int res; in octeontx_pko_dq_close() local
156 return res; in octeontx_pko_dq_close()
170 gdq = res; in octeontx_pko_dq_drain()
273 int res; in octeontx_pko_channel_open() local
276 if (res < 0) in octeontx_pko_channel_open()
286 int res; in octeontx_pko_channel_close() local
289 if (res < 0) in octeontx_pko_channel_close()
343 int res; in octeontx_pko_chan_stop() local
472 int res; in octeontx_pko_send_mtu() local
483 if (res < 0) in octeontx_pko_send_mtu()
[all …]
|
| H A D | octeontx_pkivf.h | 259 int res; in octeontx_pki_port_modify_qos() local
269 if (res < 0) in octeontx_pki_port_modify_qos()
272 return res; in octeontx_pki_port_modify_qos()
279 int res; in octeontx_pki_port_delete_qos() local
292 return res; in octeontx_pki_port_delete_qos()
299 int res; in octeontx_pki_port_close() local
314 return res; in octeontx_pki_port_close()
321 int res; in octeontx_pki_port_start() local
336 return res; in octeontx_pki_port_start()
343 int res; in octeontx_pki_port_stop() local
[all …]
|
| /dpdk/examples/vm_power_manager/ |
| H A D | vm_power_cli.c | 141 if (set_pcpu(res->vm_name, res->vcpu, res->core) == 0) in cmd_set_pcpu_parsed()
143 "%"PRId8")\n", res->vcpu, res->core); in cmd_set_pcpu_parsed()
146 "%"PRId8")\n", res->vcpu, res->core); in cmd_set_pcpu_parsed()
189 if (add_vm(res->vm_name) < 0) in cmd_vm_op_parsed()
238 remaining = res->channel_list; in cmd_channels_op_parsed()
265 res->vm_name); in cmd_channels_op_parsed()
311 res->vm_name); in cmd_set_query_parsed()
315 res->vm_name); in cmd_set_query_parsed()
444 res->core_num); in cmd_show_cpu_freq_parsed()
483 if (!strcmp(res->cmd , "up")) in cmd_set_cpu_freq_parsed()
[all …]
|
| /dpdk/lib/net/ |
| H A D | net_crc_avx512.c | 130 res = _mm_xor_si128(res, res1); in done_128()
133 res = _mm_slli_si128(res, 4); in done_128()
135 res = _mm_xor_si128(res, res1); in done_128()
236 res = _mm_xor_si128(res, d); in crc32_eth_calc_vpclmulqdq()
251 res = _mm_xor_si128(res, d); in crc32_eth_calc_vpclmulqdq()
260 res = _mm_xor_si128(res, d); in crc32_eth_calc_vpclmulqdq()
265 res = _mm_xor_si128(res, d); in crc32_eth_calc_vpclmulqdq()
272 res = _mm_slli_si128(res, 5); in crc32_eth_calc_vpclmulqdq()
275 res = _mm_slli_si128(res, 6); in crc32_eth_calc_vpclmulqdq()
278 res = _mm_slli_si128(res, 7); in crc32_eth_calc_vpclmulqdq()
[all …]
|
| /dpdk/app/test-pmd/ |
| H A D | cmdline.c | 4464 tx_qinq_set(res->port_id, res->vlan_id, res->vlan_id_outer); in cmd_tx_vlan_set_qinq_parsed()
8685 port_reg_set(res->port_id, res->reg_off, res->value); in cmd_write_reg_parsed()
8731 res->bit1_pos, res->bit2_pos, res->value); in cmd_write_reg_bit_field_parsed()
8790 port_reg_bit_set(res->port_id, res->reg_off, res->bit_pos, res->value); in cmd_write_reg_bit_parsed()
11522 res->vf_id, res->vlan_id); in cmd_set_vf_vlan_insert_parsed()
12318 res->idx, res->an, res->pn, key) : in cmd_set_macsec_sa_parsed()
12320 res->idx, res->an, res->pn, key); in cmd_set_macsec_sa_parsed()
12811 res->vf_id, res->bw); in cmd_vf_max_bw_parsed()
12819 res->vf_id, res->bw); in cmd_vf_max_bw_parsed()
13029 res->tc_no, res->bw); in cmd_vf_tc_max_bw_parsed()
[all …]
|
| H A D | bpf_cmd.c | 95 struct cmd_bpf_ld_result *res; in cmd_operate_bpf_ld_parsed() local
99 res = parsed_result; in cmd_operate_bpf_ld_parsed()
105 fname = res->prm; in cmd_operate_bpf_ld_parsed()
108 if (strcmp(res->dir, "rx") == 0) { in cmd_operate_bpf_ld_parsed()
109 rc = rte_bpf_eth_rx_elf_load(res->port, res->queue, &prm, in cmd_operate_bpf_ld_parsed()
113 rc = rte_bpf_eth_tx_elf_load(res->port, res->queue, &prm, in cmd_operate_bpf_ld_parsed()
164 struct cmd_bpf_unld_result *res; in cmd_operate_bpf_unld_parsed() local
166 res = parsed_result; in cmd_operate_bpf_unld_parsed()
168 if (strcmp(res->dir, "rx") == 0) in cmd_operate_bpf_unld_parsed()
169 rte_bpf_eth_rx_unload(res->port, res->queue); in cmd_operate_bpf_unld_parsed()
[all …]
|
| H A D | cmdline_tm.c | 1700 res->priority, res->weight, res->level_id, in cmd_add_port_tm_nonleaf_node_parsed()
1859 if (res->n_sp_priorities) in cmd_add_port_tm_nonleaf_node_pmode_parsed()
1866 res->priority, res->weight, res->level_id, in cmd_add_port_tm_nonleaf_node_pmode_parsed()
2030 res->priority, res->weight, res->level_id, in cmd_add_port_tm_leaf_node_parsed()
2489 int green = res->green; in cmd_port_tm_mark_ip_ecn_parsed()
2490 int yellow = res->yellow; in cmd_port_tm_mark_ip_ecn_parsed()
2491 int red = res->red; in cmd_port_tm_mark_ip_ecn_parsed()
2576 int green = res->green; in cmd_port_tm_mark_ip_dscp_parsed()
2578 int red = res->red; in cmd_port_tm_mark_ip_dscp_parsed()
2663 int green = res->green; in cmd_port_tm_mark_vlan_dei_parsed()
[all …]
|
| H A D | cmdline_mtr.c | 227 uint16_t port_id = res->port_id; in cmd_show_port_meter_cap_parsed()
363 uint16_t port_id = res->port_id; in cmd_add_port_meter_profile_srtcm_parsed()
372 mp.srtcm_rfc2697.cir = res->cir; in cmd_add_port_meter_profile_srtcm_parsed()
777 uint32_t mtr_id = res->mtr_id; in cmd_create_port_meter_parsed()
778 uint32_t shared = res->shared; in cmd_create_port_meter_parsed()
870 uint32_t mtr_id = res->mtr_id; in cmd_enable_port_meter_parsed()
931 uint32_t mtr_id = res->mtr_id; in cmd_disable_port_meter_parsed()
1057 uint32_t mtr_id = res->mtr_id; in cmd_del_port_meter_parsed()
1129 uint32_t mtr_id = res->mtr_id; in cmd_set_port_meter_profile_parsed()
1283 uint32_t mtr_id = res->mtr_id; in cmd_set_port_meter_stats_mask_parsed()
[all …]
|
| /dpdk/lib/cmdline/ |
| H A D | cmdline_parse_num.c | 63 *res = (uint64_t) (*res * base + c); in add_to_res()
262 if (res) *(int8_t *)res = (int8_t) res1; in cmdline_parse_num()
265 if (res) *(int16_t *)res = (int16_t) res1; in cmdline_parse_num()
268 if (res) *(int32_t *)res = (int32_t) res1; in cmdline_parse_num()
271 if (res) *(int64_t *)res = (int64_t) res1; in cmdline_parse_num()
274 if (res) *(uint8_t *)res = (uint8_t) res1; in cmdline_parse_num()
277 if (res) *(uint16_t *)res = (uint16_t) res1; in cmdline_parse_num()
280 if (res) *(uint32_t *)res = (uint32_t) res1; in cmdline_parse_num()
283 if (res) *(uint64_t *)res = res1; in cmdline_parse_num()
293 if (res) *(int8_t *)res = (int8_t) (-res1); in cmdline_parse_num()
[all …]
|
| /dpdk/lib/fib/ |
| H A D | dir24_8_avx512.c | 18 __m512i ip_vec, idxes, res, bytes; in dir24_8_vec_lookup_x16() local
40 res = _mm512_and_epi32(res, res_msk); in dir24_8_vec_lookup_x16()
43 res = _mm512_and_epi32(res, res_msk); in dir24_8_vec_lookup_x16()
51 idxes = _mm512_srli_epi32(res, 1); in dir24_8_vec_lookup_x16()
67 res = _mm512_mask_blend_epi32(msk_ext, res, idxes); in dir24_8_vec_lookup_x16()
70 res = _mm512_srli_epi32(res, 1); in dir24_8_vec_lookup_x16()
87 __m512i res, idxes, bytes; in dir24_8_vec_lookup_x8_8b() local
103 idxes = _mm512_srli_epi64(res, 1); in dir24_8_vec_lookup_x8_8b()
110 res = _mm512_mask_blend_epi64(msk_ext, res, idxes); in dir24_8_vec_lookup_x8_8b()
113 res = _mm512_srli_epi64(res, 1); in dir24_8_vec_lookup_x8_8b()
[all …]
|
| /dpdk/drivers/net/octeontx/ |
| H A D | octeontx_ethdev.c | 112 int res; in octeontx_port_open() local
114 res = 0; in octeontx_port_open()
151 return res; in octeontx_port_open()
215 int res; in octeontx_link_status_poll() local
274 int res; in octeontx_port_promisc_set() local
276 res = 0; in octeontx_port_promisc_set()
300 int res; in octeontx_port_stats() local
722 int res; in octeontx_port_link_status() local
750 int res; in octeontx_dev_link_update() local
896 int res; in octeontx_vf_start_tx_queue() local
[all …]
|
| /dpdk/app/test/ |
| H A D | commands.c | 67 if (!strcmp(res->autotest, t->command)) in cmd_autotest_parsed()
115 struct cmd_dump_result *res = parsed_result; in cmd_dump_parsed() local
117 if (!strcmp(res->dump, "dump_physmem")) in cmd_dump_parsed()
119 else if (!strcmp(res->dump, "dump_memzone")) in cmd_dump_parsed()
123 else if (!strcmp(res->dump, "dump_ring")) in cmd_dump_parsed()
171 if (!strcmp(res->dump, "dump_ring")) { in cmd_dump_one_parsed()
173 r = rte_ring_lookup(res->name); in cmd_dump_one_parsed()
182 mp = rte_mempool_lookup(res->name); in cmd_dump_one_parsed()
248 if (test_set_rxtx_conf(res->mode) < 0) in cmd_set_rxtx_parsed()
284 if (test_set_rxtx_anchor(res->type) < 0) in cmd_set_rxtx_anchor_parsed()
[all …]
|
| /dpdk/drivers/mempool/octeontx/ |
| H A D | octeontx_fpavf.c | 205 if (res->sz128 == 0 || res->domain_id == (uint16_t)~0 || in octeontx_fpa_handle_valid()
466 if (res && res->sz128 != 0) { in octeontx_gpool_free()
488 return res ? FPA_CACHE_LINE_2_OBJSZ(res->sz128) : 0; in octeontx_fpa_bufpool_block_size()
529 int res; in octeontx_fpa_bufpool_create() local
546 errno = res; in octeontx_fpa_bufpool_create()
551 gpool = res; in octeontx_fpa_bufpool_create()
565 if (res < 0) { in octeontx_fpa_bufpool_create()
566 errno = res; in octeontx_fpa_bufpool_create()
573 errno = res; in octeontx_fpa_bufpool_create()
778 int res; in fpavf_probe() local
[all …]
|
| /dpdk/drivers/event/octeontx/ |
| H A D | timvf_probe.c | 75 struct timvf_res *res = NULL; in timvf_bar() local
85 res = &tdev.rings[i]; in timvf_bar()
89 if (res == NULL) in timvf_bar()
94 return res->bar0; in timvf_bar()
96 return res->bar4; in timvf_bar()
107 struct timvf_res *res; in timvf_probe() local
131 res = &tdev.rings[tdev.total_timvfs]; in timvf_probe()
132 res->vfid = vfid; in timvf_probe()
133 res->bar0 = pci_dev->mem_resource[0].addr; in timvf_probe()
136 res->domain = (val >> 7) & 0xffff; in timvf_probe()
[all …]
|
| H A D | ssovf_probe.c | 141 struct ssowvf_res *res; in ssowvf_probe() local
174 res = &sdev.hws[vfid]; in ssowvf_probe()
175 res->vfid = vfid; in ssowvf_probe()
179 res->domain = id->domain; in ssowvf_probe()
185 res->domain)) { in ssowvf_probe()
193 res->vfid, sdev.total_ssowvfs); in ssowvf_probe()
223 struct ssovf_res *res; in ssovf_probe() local
251 res = &sdev.grp[vfid]; in ssovf_probe()
252 res->vfid = vfid; in ssovf_probe()
255 res->domain = val & 0xffff; in ssovf_probe()
[all …]
|
| /dpdk/examples/qos_sched/ |
| H A D | cmdline.c | 100 if (!strcmp(res->param_string, "period")) in cmd_setqavg_parsed()
101 qavg_period = res->number; in cmd_setqavg_parsed()
102 else if (!strcmp(res->param_string, "n")) in cmd_setqavg_parsed()
103 qavg_ntimes = res->number; in cmd_setqavg_parsed()
176 if (subport_stat(res->port_number, res->subport_number) < 0) in cmd_subportstats_parsed()
227 if (pipe_stat(res->port_number, res->subport_number, res->pipe_number) < 0) in cmd_pipestats_parsed()
290 …if (qavg_q(res->port_number, res->subport_number, res->pipe_number, res->tc_number, res->q_number)… in cmd_avg_q_parsed()
367 … if (qavg_tcpipe(res->port_number, res->subport_number, res->pipe_number, res->tc_number) < 0) in cmd_avg_tcpipe_parsed()
434 if (qavg_pipe(res->port_number, res->subport_number, res->pipe_number) < 0) in cmd_avg_pipe_parsed()
493 if (qavg_tcsubport(res->port_number, res->subport_number, res->tc_number) < 0) in cmd_avg_tcsubport_parsed()
[all …]
|
| /dpdk/devtools/ |
| H A D | checkpatches.sh | 53 res=0
62 "$1" || res=1
70 "$1" || res=1
78 "$1" || res=1
161 return $res
165 res=0
189 }' || res=1
191 return $res
195 res=0
220 }' || res=1
[all …]
|
| /dpdk/examples/cmdline/ |
| H A D | commands.c | 73 if (res->obj->ip.family == AF_INET) in cmd_obj_del_show_parsed()
75 NIPQUAD(res->obj->ip.addr.ipv4)); in cmd_obj_del_show_parsed()
78 NIP6(res->obj->ip.addr.ipv6)); in cmd_obj_del_show_parsed()
80 if (strcmp(res->action, "del") == 0) { in cmd_obj_del_show_parsed()
83 res->obj->name, ip_str); in cmd_obj_del_show_parsed()
84 free(res->obj); in cmd_obj_del_show_parsed()
86 else if (strcmp(res->action, "show") == 0) { in cmd_obj_del_show_parsed()
88 res->obj->name, ip_str); in cmd_obj_del_show_parsed()
128 if (!strcmp(res->name, o->name)) { in cmd_obj_add_parsed()
140 strlcpy(o->name, res->name, sizeof(o->name)); in cmd_obj_add_parsed()
[all …]
|
| /dpdk/drivers/bus/pci/windows/ |
| H A D | pci_netuio.c | 25 BOOL res; in send_ioctl() local
28 res = DeviceIoControl(f, ioctl, in_buf, in_buf_size, in send_ioctl()
30 if (!res) { in send_ioctl()
42 BOOL res; in get_netuio_device_information_set() local
48 res = SetupDiGetDeviceInstanceId(dev_info, dev_info_data, in get_netuio_device_information_set()
50 if (!res) { in get_netuio_device_information_set()
69 BOOL res; in get_netuio_device_interface_detail() local
79 if (!res) { in get_netuio_device_interface_detail()
88 if (!res) { in get_netuio_device_interface_detail()
103 res = SetupDiGetDeviceInterfaceDetail(di_set, &dev_ifx_data, in get_netuio_device_interface_detail()
[all …]
|
| /dpdk/lib/eal/common/ |
| H A D | eal_common_string_fns.c | 50 size_t res = 0; in rte_strscpy() local
54 dst[res] = src[res]; in rte_strscpy()
55 if (src[res] == '\0') in rte_strscpy()
56 return res; in rte_strscpy()
57 res++; in rte_strscpy()
62 if (res != 0) in rte_strscpy()
63 dst[res - 1] = '\0'; in rte_strscpy()
|
| /dpdk/examples/vm_power_manager/guest_cli/ |
| H A D | vm_power_cli_guest.c | 191 if (!strcmp(res->cpu_num, "all")) { in cmd_query_freq_list_parsed()
209 ep == res->cpu_num) { in cmd_query_freq_list_parsed()
301 if (!strcmp(res->cpu_num, "all")) { in cmd_query_caps_list_parsed()
319 ep == res->cpu_num) { in cmd_query_caps_list_parsed()
415 if (!strcmp(res->cmd, "up")) in cmd_set_cpu_freq_parsed()
416 ret = rte_power_freq_up(res->lcore_id); in cmd_set_cpu_freq_parsed()
417 else if (!strcmp(res->cmd, "down")) in cmd_set_cpu_freq_parsed()
419 else if (!strcmp(res->cmd, "min")) in cmd_set_cpu_freq_parsed()
420 ret = rte_power_freq_min(res->lcore_id); in cmd_set_cpu_freq_parsed()
421 else if (!strcmp(res->cmd, "max")) in cmd_set_cpu_freq_parsed()
[all …]
|