| /linux/tools/testing/selftests/x86/ |
| A D | amx.c | 705 pthread_mutex_lock(&finfo->mutex); in check_tiledata()
733 return finfo; in check_tiledata()
743 finfo[i].nr = i; in create_threads()
750 pthread_mutex_lock(&finfo[i].mutex); in create_threads()
753 finfo[i].next = &finfo[next_nr]; in create_threads()
755 if (pthread_create(&finfo[i].thread, NULL, check_tiledata, &finfo[i])) in create_threads()
774 struct futex_info *finfo; in test_context_switch() local
787 finfo = malloc(sizeof(*finfo) * ctxtswtest_config.num_threads); in test_context_switch()
788 if (!finfo) in test_context_switch()
816 if (thread_retval != &finfo[i]) in test_context_switch()
[all …]
|
| /linux/drivers/mailbox/ |
| A D | omap-mailbox.c | 744 finfo = finfoblk; in omap_mbox_probe()
752 finfo->tx_id = tmp[0]; in omap_mbox_probe()
753 finfo->tx_irq = tmp[1]; in omap_mbox_probe()
754 finfo->tx_usr = tmp[2]; in omap_mbox_probe()
760 finfo->rx_id = tmp[0]; in omap_mbox_probe()
761 finfo->rx_irq = tmp[1]; in omap_mbox_probe()
762 finfo->rx_usr = tmp[2]; in omap_mbox_probe()
769 if (finfo->tx_id >= num_fifos || finfo->rx_id >= num_fifos || in omap_mbox_probe()
770 finfo->tx_usr >= num_users || finfo->rx_usr >= num_users) in omap_mbox_probe()
804 finfo = finfoblk; in omap_mbox_probe()
[all …]
|
| /linux/drivers/hid/usbhid/ |
| A D | hiddev.c | 601 struct hiddev_field_info finfo; in hiddev_ioctl() local
749 if (copy_from_user(&finfo, user_arg, sizeof(finfo))) { in hiddev_ioctl()
755 rinfo.report_id = finfo.report_id; in hiddev_ioctl()
763 finfo.field_index = array_index_nospec(finfo.field_index, in hiddev_ioctl()
767 memset(&finfo, 0, sizeof(finfo)); in hiddev_ioctl()
771 finfo.maxusage = field->maxusage; in hiddev_ioctl()
772 finfo.flags = field->flags; in hiddev_ioctl()
773 finfo.physical = field->physical; in hiddev_ioctl()
774 finfo.logical = field->logical; in hiddev_ioctl()
781 finfo.unit = field->unit; in hiddev_ioctl()
[all …]
|
| /linux/drivers/gpu/drm/tidss/ |
| A D | tidss_plane.c | 30 const struct drm_format_info *finfo; in tidss_plane_atomic_check() local
70 finfo = drm_format_info(new_plane_state->fb->format->format); in tidss_plane_atomic_check()
72 if ((new_plane_state->src_x >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
75 __func__, (new_plane_state->src_x >> 16), finfo->hsub); in tidss_plane_atomic_check()
79 if ((new_plane_state->src_y >> 16) % finfo->vsub != 0) { in tidss_plane_atomic_check()
82 __func__, (new_plane_state->src_y >> 16), finfo->vsub); in tidss_plane_atomic_check()
86 if ((new_plane_state->src_w >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
90 finfo->hsub); in tidss_plane_atomic_check()
|
| /linux/drivers/fpga/ |
| A D | dfl.c | 798 feature->id = finfo->fid; in build_info_commit_dev()
820 if (finfo->nr_irqs) { in build_info_commit_dev()
834 list_del(&finfo->node); in build_info_commit_dev()
835 kfree(finfo); in build_info_commit_dev()
904 list_del(&finfo->node); in build_info_free()
905 kfree(finfo); in build_info_free()
1042 finfo = kzalloc(sizeof(*finfo), GFP_KERNEL); in create_feature_instance()
1043 if (!finfo) in create_feature_instance()
1046 finfo->fid = fid; in create_feature_instance()
1049 finfo->mmio_res.end = finfo->mmio_res.start + size - 1; in create_feature_instance()
[all …]
|
| /linux/drivers/scsi/aic7xxx/aicasm/ |
| A D | aicasm_symbol.c | 105 if (symbol->info.finfo != NULL) { in symbol_delete()
106 symlist_free(&symbol->info.finfo->symrefs); in symbol_delete()
107 free(symbol->info.finfo); in symbol_delete()
259 && (curnode->symbol->info.finfo->value > in symlist_add()
260 newnode->symbol->info.finfo->value)))) in symlist_add()
279 && (cursymbol->info.finfo->value > in symlist_add()
280 symbol->info.finfo->value)))) in symlist_add()
455 curnode->symbol->info.finfo->value, in aic_print_reg_dump_entry()
456 curnode->symbol->info.finfo->mask); in aic_print_reg_dump_entry()
582 regnode = SLIST_FIRST(&curnode->symbol->info.finfo->symrefs); in symtable_dump()
[all …]
|
| A D | aicasm_gram.y | 710 $$.value = symbol->info.finfo->value;
1433 sym->info.finfo->value = value;
1439 sym->info.finfo->value = value;
1440 sym->info.finfo->mask = value;
1442 sym->info.finfo->mask = field_symbol->info.finfo->value;
1444 sym->info.finfo->mask = 0xFF;
1450 } else if (value != sym->info.finfo->value) {
1455 if (symlist_search(&(sym->info.finfo->symrefs),
1513 symbol->info.finfo = in initialize_symbol()
1515 if (symbol->info.finfo == NULL) { in initialize_symbol()
[all …]
|
| A D | aicasm_symbol.h | 130 struct field_info *finfo; member
|
| /linux/drivers/gpu/drm/ingenic/ |
| A D | ingenic-ipu.c | 293 const struct drm_format_info *finfo; in ingenic_ipu_plane_atomic_update() local
301 finfo = drm_format_info(newstate->fb->format->format); in ingenic_ipu_plane_atomic_update()
328 if (finfo->num_planes > 1) in ingenic_ipu_plane_atomic_update()
331 if (finfo->num_planes > 2) in ingenic_ipu_plane_atomic_update()
343 if (finfo->num_planes == 1) in ingenic_ipu_plane_atomic_update()
349 if (finfo->num_planes > 2) in ingenic_ipu_plane_atomic_update()
350 stride = ((newstate->src_w >> 16) * finfo->cpp[2] / finfo->hsub) in ingenic_ipu_plane_atomic_update()
353 if (finfo->num_planes > 1) in ingenic_ipu_plane_atomic_update()
354 stride |= ((newstate->src_w >> 16) * finfo->cpp[1] / finfo->hsub) in ingenic_ipu_plane_atomic_update()
366 switch (finfo->format) { in ingenic_ipu_plane_atomic_update()
[all …]
|
| /linux/drivers/net/ethernet/cavium/liquidio/ |
| A D | lio_vf_main.c | 811 skb = finfo->skb; in free_netbuf()
812 lio = finfo->lio; in free_netbuf()
833 skb = finfo->skb; in free_netsgbuf()
834 lio = finfo->lio; in free_netsgbuf()
835 g = finfo->g; in free_netsgbuf()
878 lio = finfo->lio; in free_netsgbuf_with_resp()
879 g = finfo->g; in free_netsgbuf_with_resp()
1326 lio = finfo->lio; in handle_timestamp()
1327 sc = finfo->sc; in handle_timestamp()
1374 finfo->sc = sc; in send_nic_timestamp_pkt()
[all …]
|
| A D | lio_main.c | 1426 skb = finfo->skb; in free_netbuf()
1427 lio = finfo->lio; in free_netbuf()
1448 skb = finfo->skb; in free_netsgbuf()
1449 lio = finfo->lio; in free_netsgbuf()
1450 g = finfo->g; in free_netsgbuf()
1492 lio = finfo->lio; in free_netsgbuf_with_resp()
1493 g = finfo->g; in free_netsgbuf_with_resp()
2198 lio = finfo->lio; in handle_timestamp()
2199 sc = finfo->sc; in handle_timestamp()
2248 finfo->sc = sc; in send_nic_timestamp_pkt()
[all …]
|
| A D | lio_core.c | 196 struct octnet_buf_free_info *finfo; in octeon_update_tx_completion_counters() local
203 finfo = buf; in octeon_update_tx_completion_counters()
204 skb = finfo->skb; in octeon_update_tx_completion_counters()
223 struct octnet_buf_free_info *finfo; in octeon_report_sent_bytes_to_bql() local
231 finfo = buf; in octeon_report_sent_bytes_to_bql()
232 skb = finfo->skb; in octeon_report_sent_bytes_to_bql()
|
| /linux/drivers/firmware/efi/libstub/ |
| A D | file.c | 32 struct finfo { struct
38 struct finfo *fi, in efi_open_file() argument
53 info_sz = sizeof(struct finfo); in efi_open_file()
159 struct finfo fi; in handle_cmdline_files()
|
| /linux/drivers/media/usb/ttusb-dec/ |
| A D | ttusb_dec.c | 561 struct filter_info *finfo; in ttusb_dec_process_filter() local
571 if (finfo->stream_id == sid) { in ttusb_dec_process_filter()
572 filter = finfo->filter; in ttusb_dec_process_filter()
1047 struct filter_info *finfo; in ttusb_dec_start_sec_feed() local
1067 finfo->stream_id = c[1]; in ttusb_dec_start_sec_feed()
1076 dvbdmxfeed->priv = finfo; in ttusb_dec_start_sec_feed()
1134 b0[1] = finfo->stream_id; in ttusb_dec_stop_sec_feed()
1136 list_del(&finfo->filter_info_list); in ttusb_dec_stop_sec_feed()
1138 kfree(finfo); in ttusb_dec_stop_sec_feed()
1615 struct filter_info *finfo; in ttusb_dec_exit_filters() local
[all …]
|
| /linux/drivers/mtd/chips/ |
| A D | jedec_probe.c | 2050 mfr = (uint8_t)finfo->mfr_id; in jedec_match()
2051 id = (uint8_t)finfo->dev_id; in jedec_match()
2057 if (finfo->dev_id > 0xff) { in jedec_match()
2064 mfr = (uint16_t)finfo->mfr_id; in jedec_match()
2065 id = (uint16_t)finfo->dev_id; in jedec_match()
2068 mfr = (uint16_t)finfo->mfr_id; in jedec_match()
2069 id = (uint32_t)finfo->dev_id; in jedec_match()
2083 __func__, base, 1 << finfo->dev_size, base + (1 << finfo->dev_size) ); in jedec_match()
2086 __func__, finfo->mfr_id, finfo->dev_id, in jedec_match()
2087 1 << finfo->dev_size ); in jedec_match()
[all …]
|
| /linux/fs/nilfs2/ |
| A D | recovery.c | 328 struct nilfs_finfo *finfo; in nilfs_scan_dsync_log() local
330 finfo = nilfs_read_summary_info(nilfs, &bh, &offset, in nilfs_scan_dsync_log()
331 sizeof(*finfo)); in nilfs_scan_dsync_log()
332 if (unlikely(!finfo)) in nilfs_scan_dsync_log()
335 ino = le64_to_cpu(finfo->fi_ino); in nilfs_scan_dsync_log()
336 nblocks = le32_to_cpu(finfo->fi_nblocks); in nilfs_scan_dsync_log()
337 ndatablk = le32_to_cpu(finfo->fi_ndatablk); in nilfs_scan_dsync_log()
|
| A D | segment.c | 494 struct nilfs_finfo *finfo; in nilfs_segctor_end_finfo() local
512 sizeof(*finfo)); in nilfs_segctor_end_finfo()
513 finfo->fi_ino = cpu_to_le64(inode->i_ino); in nilfs_segctor_end_finfo()
516 finfo->fi_cno = cpu_to_le64(cno); in nilfs_segctor_end_finfo()
1552 struct nilfs_finfo *finfo = NULL; in nilfs_segctor_update_payload_blocknr() local
1568 if (!finfo) { in nilfs_segctor_update_payload_blocknr()
1569 finfo = nilfs_segctor_map_segsum_entry( in nilfs_segctor_update_payload_blocknr()
1570 sci, &ssp, sizeof(*finfo)); in nilfs_segctor_update_payload_blocknr()
1571 ino = le64_to_cpu(finfo->fi_ino); in nilfs_segctor_update_payload_blocknr()
1572 nblocks = le32_to_cpu(finfo->fi_nblocks); in nilfs_segctor_update_payload_blocknr()
[all …]
|
| /linux/drivers/gpu/drm/ |
| A D | drm_fb_cma_helper.c | 119 const struct drm_format_info *finfo = state->fb->format; in drm_fb_cma_sync_non_coherent() local
127 for (i = 0; i < finfo->num_planes; i++) { in drm_fb_cma_sync_non_coherent()
|
| /linux/drivers/net/wireless/realtek/rtw89/ |
| A D | coex.c | 1024 pfwinfo->rpt_fbtc_tdma.finfo.type, in _chk_btc_report()
1030 pfwinfo->rpt_fbtc_tdma.finfo.rsvd0, in _chk_btc_report()
1036 &pfwinfo->rpt_fbtc_tdma.finfo, in _chk_btc_report()
1050 &pfwinfo->rpt_fbtc_slots.finfo.slot[i]; in _chk_btc_report()
1073 pfwinfo->rpt_fbtc_slots.finfo.slot, in _chk_btc_report()
1101 prpt = &pfwinfo->rpt_ctrl.finfo; in _chk_btc_report()
5127 t = &pfwinfo->rpt_fbtc_tdma.finfo; in _show_fbtc_tdma()
5144 s = pfwinfo->rpt_fbtc_slots.finfo.slot; in _show_fbtc_tdma()
5350 ns = &pfwinfo->rpt_fbtc_nullsta.finfo; in _show_fbtc_nullsta()
5388 pstep = &pfwinfo->rpt_fbtc_step.finfo; in _show_fbtc_step()
[all …]
|
| A D | core.h | 1620 struct rtw89_btc_fbtc_rpt_ctrl finfo; /* info from fw */ member
1625 struct rtw89_btc_fbtc_tdma finfo; /* info from fw */ member
1630 struct rtw89_btc_fbtc_slots finfo; /* info from fw */ member
1635 struct rtw89_btc_fbtc_cysta finfo; /* info from fw */ member
1640 struct rtw89_btc_fbtc_steps finfo; /* info from fw */ member
1645 struct rtw89_btc_fbtc_cynullsta finfo; /* info from fw */ member
1650 struct rtw89_btc_fbtc_mreg_val finfo; /* info from fw */ member
1655 struct rtw89_btc_fbtc_gpio_dbg finfo; /* info from fw */ member
1660 struct rtw89_btc_fbtc_btver finfo; /* info from fw */ member
1665 struct rtw89_btc_fbtc_btscan finfo; /* info from fw */ member
[all …]
|
| /linux/drivers/iommu/ |
| A D | exynos-iommu.c | 386 const struct sysmmu_fault_info *finfo, in show_fault_information() argument
392 dev_name(data->master), finfo->name, fault_addr); in show_fault_information()
406 const struct sysmmu_fault_info *finfo; in exynos_sysmmu_irq() local
417 finfo = sysmmu_faults; in exynos_sysmmu_irq()
422 finfo = sysmmu_v5_faults; in exynos_sysmmu_irq()
431 for (i = 0; i < n; i++, finfo++) in exynos_sysmmu_irq()
432 if (finfo->bit == itype) in exynos_sysmmu_irq()
438 fault_addr = readl(data->sfrbase + finfo->addr_reg); in exynos_sysmmu_irq()
439 show_fault_information(data, finfo, fault_addr); in exynos_sysmmu_irq()
443 data->master, fault_addr, finfo->type); in exynos_sysmmu_irq()
|
| /linux/drivers/hv/ |
| A D | hv_balloon.c | 144 } finfo; member
996 pg_start = dm->ha_wrk.ha_page_range.finfo.start_page; in hot_add_req()
997 pfn_cnt = dm->ha_wrk.ha_page_range.finfo.page_cnt; in hot_add_req()
999 rg_start = dm->ha_wrk.ha_region_range.finfo.start_page; in hot_add_req()
1000 rg_sz = dm->ha_wrk.ha_region_range.finfo.page_cnt; in hot_add_req()
1193 int num_pages = range_array->finfo.page_cnt; in free_balloon_pages()
1194 __u64 start_frame = range_array->finfo.start_page; in free_balloon_pages()
1250 bl_resp->range_array[i].finfo.start_page = in alloc_balloon_pages()
1252 bl_resp->range_array[i].finfo.page_cnt = alloc_unit; in alloc_balloon_pages()
|
| /linux/tools/lib/bpf/ |
| A D | bpf.c | 258 void *finfo = NULL, *linfo = NULL; in libbpf__bpf_prog_load() local
315 while (errno == E2BIG && (!finfo || !linfo)) { in libbpf__bpf_prog_load()
316 if (!finfo && attr.func_info_cnt && in libbpf__bpf_prog_load()
319 finfo = alloc_zero_tailing_info(load_attr->func_info, in libbpf__bpf_prog_load()
323 if (!finfo) { in libbpf__bpf_prog_load()
328 attr.func_info = ptr_to_u64(finfo); in libbpf__bpf_prog_load()
365 free(finfo); in libbpf__bpf_prog_load()
|
| /linux/tools/perf/util/ |
| A D | bpf-event.c | 165 const struct bpf_func_info *finfo; in synthesize_bpf_prog_name() local
174 finfo = func_infos + sub_id * info->func_info_rec_size; in synthesize_bpf_prog_name()
175 t = btf__type_by_id(btf, finfo->type_id); in synthesize_bpf_prog_name()
|
| /linux/tools/bpf/bpftool/ |
| A D | btf_dumper.c | 38 struct bpf_func_info *finfo; in dump_prog_id_as_func_ptr() local
72 finfo = u64_to_ptr(info->func_info); in dump_prog_id_as_func_ptr()
73 func_type = btf__type_by_id(prog_btf, finfo->type_id); in dump_prog_id_as_func_ptr()
|