| /Linux-v6.1/tools/testing/selftests/x86/ |
| D | amx.c | 693 struct futex_info *finfo = (struct futex_info *)info; in check_tiledata() local
707 pthread_mutex_lock(&finfo->mutex); in check_tiledata()
727 pthread_mutex_unlock(&finfo->next->mutex); in check_tiledata()
735 return finfo; in check_tiledata()
738 static int create_threads(int num, struct futex_info *finfo) in create_threads() argument
745 finfo[i].nr = i; in create_threads()
751 pthread_mutex_init(&finfo[i].mutex, NULL); in create_threads()
752 pthread_mutex_lock(&finfo[i].mutex); in create_threads()
755 finfo[i].next = &finfo[next_nr]; in create_threads()
757 if (pthread_create(&finfo[i].thread, NULL, check_tiledata, &finfo[i])) in create_threads()
[all …]
|
| /Linux-v6.1/drivers/mailbox/ |
| D | omap-mailbox.c | 705 struct omap_mbox_fifo_info *finfo, *finfoblk; in omap_mbox_probe() local
744 finfo = finfoblk; in omap_mbox_probe()
746 for (i = 0; i < info_count; i++, finfo++) { 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()
764 finfo->name = child->name; in omap_mbox_probe()
[all …]
|
| /Linux-v6.1/tools/testing/selftests/vm/ |
| D | khugepaged.c | 82 static struct file_info finfo; variable
348 if (file_ops && finfo.type == VMA_FILE) in write_settings()
349 _write_num(finfo.dev_queue_read_ahead_path, in write_settings()
421 if (file_ops && finfo.type == VMA_FILE) in save_settings()
423 _read_num(finfo.dev_queue_read_ahead_path); in save_settings()
441 finfo.dir = dir; in get_finfo()
442 stat(finfo.dir, &path_stat); in get_finfo()
444 printf("%s: Not a directory (%s)\n", __func__, finfo.dir); in get_finfo()
447 if (snprintf(finfo.path, sizeof(finfo.path), "%s/" TEST_FILE, in get_finfo()
448 finfo.dir) >= sizeof(finfo.path)) { in get_finfo()
[all …]
|
| /Linux-v6.1/drivers/hid/usbhid/ |
| 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()
754 rinfo.report_type = finfo.report_type; in hiddev_ioctl()
755 rinfo.report_id = finfo.report_id; in hiddev_ioctl()
761 if (finfo.field_index >= report->maxfield) in hiddev_ioctl()
763 finfo.field_index = array_index_nospec(finfo.field_index, in hiddev_ioctl()
766 field = report->field[finfo.field_index]; in hiddev_ioctl()
767 memset(&finfo, 0, sizeof(finfo)); in hiddev_ioctl()
768 finfo.report_type = rinfo.report_type; in hiddev_ioctl()
769 finfo.report_id = rinfo.report_id; in hiddev_ioctl()
[all …]
|
| /Linux-v6.1/drivers/gpu/drm/tidss/ |
| D | tidss_plane.c | 31 const struct drm_format_info *finfo; in tidss_plane_atomic_check() local
71 finfo = drm_format_info(new_plane_state->fb->format->format); in tidss_plane_atomic_check()
73 if ((new_plane_state->src_x >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
76 __func__, (new_plane_state->src_x >> 16), finfo->hsub); in tidss_plane_atomic_check()
80 if ((new_plane_state->src_y >> 16) % finfo->vsub != 0) { in tidss_plane_atomic_check()
83 __func__, (new_plane_state->src_y >> 16), finfo->vsub); in tidss_plane_atomic_check()
87 if ((new_plane_state->src_w >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
91 finfo->hsub); in tidss_plane_atomic_check()
|
| /Linux-v6.1/drivers/fpga/ |
| D | dfl.c | 747 struct dfl_feature_info *finfo, *p; in build_info_commit_dev() local
791 list_for_each_entry_safe(finfo, p, &binfo->sub_features, node) { in build_info_commit_dev()
798 feature->id = finfo->fid; in build_info_commit_dev()
799 feature->revision = finfo->revision; in build_info_commit_dev()
812 &finfo->mmio_res); in build_info_commit_dev()
817 fdev->resource[res_idx++] = finfo->mmio_res; in build_info_commit_dev()
820 if (finfo->nr_irqs) { in build_info_commit_dev()
821 ctx = devm_kcalloc(binfo->dev, finfo->nr_irqs, in build_info_commit_dev()
826 for (i = 0; i < finfo->nr_irqs; i++) in build_info_commit_dev()
828 binfo->irq_table[finfo->irq_base + i]; in build_info_commit_dev()
[all …]
|
| /Linux-v6.1/drivers/scsi/aic7xxx/aicasm/ |
| 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 …]
|
| 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),
1460 symlist_add(&(sym->info.finfo->symrefs), cur_symbol,
1462 cur_symbol->info.rinfo->valid_bitmask |= sym->info.finfo->mask;
[all …]
|
| D | aicasm_symbol.h | 130 struct field_info *finfo; member
|
| /Linux-v6.1/net/ipv6/ |
| D | seg6_local.c | 325 static __u8 seg6_flv_lcblock_octects(const struct seg6_flavors_info *finfo) in seg6_flv_lcblock_octects() argument
327 return finfo->lcblock_bits >> 3; in seg6_flv_lcblock_octects()
330 static __u8 seg6_flv_lcnode_func_octects(const struct seg6_flavors_info *finfo) in seg6_flv_lcnode_func_octects() argument
332 return finfo->lcnode_func_bits >> 3; in seg6_flv_lcnode_func_octects()
336 const struct seg6_flavors_info *finfo) in seg6_next_csid_is_arg_zero() argument
338 __u8 fnc_octects = seg6_flv_lcnode_func_octects(finfo); in seg6_next_csid_is_arg_zero()
339 __u8 blk_octects = seg6_flv_lcblock_octects(finfo); in seg6_next_csid_is_arg_zero()
354 const struct seg6_flavors_info *finfo) in seg6_next_csid_advance_arg() argument
356 __u8 fnc_octects = seg6_flv_lcnode_func_octects(finfo); in seg6_next_csid_advance_arg()
357 __u8 blk_octects = seg6_flv_lcblock_octects(finfo); in seg6_next_csid_advance_arg()
[all …]
|
| /Linux-v6.1/drivers/gpu/drm/ingenic/ |
| D | ingenic-ipu.c | 329 const struct drm_format_info *finfo; in ingenic_ipu_plane_atomic_update() local
342 finfo = drm_format_info(newstate->fb->format->format); in ingenic_ipu_plane_atomic_update()
369 if (finfo->num_planes > 1) in ingenic_ipu_plane_atomic_update()
372 if (finfo->num_planes > 2) in ingenic_ipu_plane_atomic_update()
384 if (finfo->num_planes == 1) in ingenic_ipu_plane_atomic_update()
390 if (finfo->num_planes > 2) in ingenic_ipu_plane_atomic_update()
391 stride = ((newstate->src_w >> 16) * finfo->cpp[2] / finfo->hsub) in ingenic_ipu_plane_atomic_update()
394 if (finfo->num_planes > 1) in ingenic_ipu_plane_atomic_update()
395 stride |= ((newstate->src_w >> 16) * finfo->cpp[1] / finfo->hsub) in ingenic_ipu_plane_atomic_update()
400 stride = ((newstate->src_w >> 16) * finfo->cpp[0]) << JZ_IPU_Y_STRIDE_Y_LSB; in ingenic_ipu_plane_atomic_update()
[all …]
|
| /Linux-v6.1/drivers/net/ethernet/cavium/liquidio/ |
| D | lio_vf_main.c | 806 struct octnet_buf_free_info *finfo; in free_netbuf() local
810 finfo = (struct octnet_buf_free_info *)buf; in free_netbuf()
811 skb = finfo->skb; in free_netbuf()
812 lio = finfo->lio; in free_netbuf()
814 dma_unmap_single(&lio->oct_dev->pci_dev->dev, finfo->dptr, skb->len, in free_netbuf()
826 struct octnet_buf_free_info *finfo; in free_netsgbuf() local
832 finfo = (struct octnet_buf_free_info *)buf; in free_netsgbuf()
833 skb = finfo->skb; in free_netsgbuf()
834 lio = finfo->lio; in free_netsgbuf()
835 g = finfo->g; in free_netsgbuf()
[all …]
|
| D | lio_main.c | 1417 struct octnet_buf_free_info *finfo; in free_netbuf() local
1420 finfo = (struct octnet_buf_free_info *)buf; in free_netbuf()
1421 skb = finfo->skb; in free_netbuf()
1422 lio = finfo->lio; in free_netbuf()
1424 dma_unmap_single(&lio->oct_dev->pci_dev->dev, finfo->dptr, skb->len, in free_netbuf()
1436 struct octnet_buf_free_info *finfo; in free_netsgbuf() local
1442 finfo = (struct octnet_buf_free_info *)buf; in free_netsgbuf()
1443 skb = finfo->skb; in free_netsgbuf()
1444 lio = finfo->lio; in free_netsgbuf()
1445 g = finfo->g; in free_netsgbuf()
[all …]
|
| /Linux-v6.1/drivers/firmware/efi/libstub/ |
| 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()
177 struct finfo fi; in handle_cmdline_files()
|
| /Linux-v6.1/drivers/media/usb/ttusb-dec/ |
| D | ttusb_dec.c | 561 struct filter_info *finfo; in ttusb_dec_process_filter() local
570 finfo = list_entry(item, struct filter_info, filter_info_list); in ttusb_dec_process_filter()
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
1063 if (!(finfo = kmalloc(sizeof(struct filter_info), in ttusb_dec_start_sec_feed()
1067 finfo->stream_id = c[1]; in ttusb_dec_start_sec_feed()
1068 finfo->filter = dvbdmxfeed->filter; in ttusb_dec_start_sec_feed()
1071 list_add_tail(&finfo->filter_info_list, in ttusb_dec_start_sec_feed()
1076 dvbdmxfeed->priv = finfo; in ttusb_dec_start_sec_feed()
[all …]
|
| /Linux-v6.1/drivers/mtd/chips/ |
| D | jedec_probe.c | 2033 const struct amd_flash_info *finfo ) in jedec_match() argument
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()
2084 if ( base + cfi_interleave(cfi) * ( 1 << finfo->dev_size ) > map->size ) { in jedec_match()
[all …]
|
| /Linux-v6.1/drivers/gpu/drm/ |
| D | drm_fb_dma_helper.c | 124 const struct drm_format_info *finfo = state->fb->format; in drm_fb_dma_sync_non_coherent() local
132 for (i = 0; i < finfo->num_planes; i++) { in drm_fb_dma_sync_non_coherent()
|
| /Linux-v6.1/fs/nilfs2/ |
| 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()
|
| D | segment.c | 494 struct nilfs_finfo *finfo; in nilfs_segctor_end_finfo() local
511 finfo = nilfs_segctor_map_segsum_entry(sci, &sci->sc_finfo_ptr, in nilfs_segctor_end_finfo()
512 sizeof(*finfo)); in nilfs_segctor_end_finfo()
513 finfo->fi_ino = cpu_to_le64(inode->i_ino); in nilfs_segctor_end_finfo()
514 finfo->fi_nblocks = cpu_to_le32(sci->sc_blk_cnt); in nilfs_segctor_end_finfo()
515 finfo->fi_ndatablk = cpu_to_le32(sci->sc_datablk_cnt); in nilfs_segctor_end_finfo()
516 finfo->fi_cno = cpu_to_le64(cno); in nilfs_segctor_end_finfo()
1561 struct nilfs_finfo *finfo = NULL; in nilfs_segctor_update_payload_blocknr() local
1577 if (!finfo) { in nilfs_segctor_update_payload_blocknr()
1578 finfo = nilfs_segctor_map_segsum_entry( in nilfs_segctor_update_payload_blocknr()
[all …]
|
| /Linux-v6.1/drivers/iommu/ |
| D | exynos-iommu.c | 456 const struct sysmmu_fault_info *finfo, in show_fault_information() argument
462 dev_name(data->master), finfo->name, fault_addr); in show_fault_information()
476 const struct sysmmu_fault_info *finfo; in exynos_sysmmu_irq() local
484 finfo = sysmmu_faults; in exynos_sysmmu_irq()
487 finfo = sysmmu_v5_faults; in exynos_sysmmu_irq()
496 for (i = 0; i < n; i++, finfo++) in exynos_sysmmu_irq()
497 if (finfo->bit == itype) in exynos_sysmmu_irq()
503 fault_addr = readl(data->sfrbase + finfo->addr_reg); in exynos_sysmmu_irq()
504 show_fault_information(data, finfo, fault_addr); in exynos_sysmmu_irq()
508 data->master, fault_addr, finfo->type); in exynos_sysmmu_irq()
|
| /Linux-v6.1/drivers/hv/ |
| D | hv_balloon.c | 146 } finfo; member
1003 pg_start = dm->ha_wrk.ha_page_range.finfo.start_page; in hot_add_req()
1004 pfn_cnt = dm->ha_wrk.ha_page_range.finfo.page_cnt; in hot_add_req()
1006 rg_start = dm->ha_wrk.ha_region_range.finfo.start_page; in hot_add_req()
1007 rg_sz = dm->ha_wrk.ha_region_range.finfo.page_cnt; in hot_add_req()
1216 int num_pages = range_array->finfo.page_cnt; in free_balloon_pages()
1217 __u64 start_frame = range_array->finfo.start_page; in free_balloon_pages()
1273 bl_resp->range_array[i].finfo.start_page = in alloc_balloon_pages()
1275 bl_resp->range_array[i].finfo.page_cnt = alloc_unit; in alloc_balloon_pages()
|
| /Linux-v6.1/drivers/net/wireless/realtek/rtw89/ |
| D | coex.c | 955 pfinfo = &pfwinfo->rpt_ctrl.finfo; in _chk_btc_report()
956 pcinfo->req_len = sizeof(pfwinfo->rpt_ctrl.finfo); in _chk_btc_report()
968 pfinfo = &pfwinfo->rpt_fbtc_tdma.finfo; in _chk_btc_report()
969 pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_tdma.finfo); in _chk_btc_report()
980 pfinfo = &pfwinfo->rpt_fbtc_slots.finfo; in _chk_btc_report()
981 pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_slots.finfo); in _chk_btc_report()
989 pfinfo = &pfwinfo->rpt_fbtc_cysta.finfo; in _chk_btc_report()
990 pcysta_le32 = &pfwinfo->rpt_fbtc_cysta.finfo; in _chk_btc_report()
992 pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_cysta.finfo); in _chk_btc_report()
1005 pfinfo = &pfwinfo->rpt_fbtc_step.finfo; in _chk_btc_report()
[all …]
|
| /Linux-v6.1/tools/bpf/bpftool/ |
| D | common.c | 336 const struct bpf_func_info finfo = {}; in get_prog_full_name() local
350 if (info.func_info_rec_size > sizeof(finfo)) in get_prog_full_name()
351 info.func_info_rec_size = sizeof(finfo); in get_prog_full_name()
352 info.func_info = ptr_to_u64(&finfo); in get_prog_full_name()
361 func_type = btf__type_by_id(prog_btf, finfo.type_id); in get_prog_full_name()
|
| /Linux-v6.1/tools/lib/bpf/ |
| D | bpf.c | 236 void *finfo = NULL, *linfo = NULL; in bpf_prog_load() local
326 while (errno == E2BIG && (!finfo || !linfo)) { in bpf_prog_load()
327 if (!finfo && attr.func_info_cnt && in bpf_prog_load()
330 finfo = alloc_zero_tailing_info(func_info, in bpf_prog_load()
334 if (!finfo) { in bpf_prog_load()
339 attr.func_info = ptr_to_u64(finfo); in bpf_prog_load()
376 free(finfo); in bpf_prog_load()
|
| /Linux-v6.1/drivers/gpu/drm/bridge/imx/ |
| D | imx8qm-ldb-drv.c | 318 const struct drm_format_info *finfo; in imx8qm_ldb_bridge_atomic_get_input_bus_fmts() local
339 finfo = drm_format_info(di->bus_formats[0]); in imx8qm_ldb_bridge_atomic_get_input_bus_fmts()
341 input_fmts[0] = finfo->depth == 18 ? in imx8qm_ldb_bridge_atomic_get_input_bus_fmts()
|
