Home
last modified time | relevance | path

Searched refs:finfo (Results 1 – 25 of 37) sorted by relevance

12

/linux/tools/testing/selftests/x86/
H A Damx.c670 struct futex_info *finfo = (struct futex_info *)info; in check_tiledata() local
684 pthread_mutex_lock(&finfo->mutex); in check_tiledata()
704 pthread_mutex_unlock(&finfo->next->mutex); in check_tiledata()
712 return finfo; in check_tiledata()
715 static int create_threads(int num, struct futex_info *finfo) in create_threads() argument
722 finfo[i].nr = i; in create_threads()
728 pthread_mutex_init(&finfo[i].mutex, NULL); in create_threads()
729 pthread_mutex_lock(&finfo[i].mutex); in create_threads()
732 finfo[i].next = &finfo[next_nr]; in create_threads()
734 if (pthread_create(&finfo[i].thread, NULL, check_tiledata, &finfo[i])) in create_threads()
[all …]
/linux/fs/netfs/
H A Dbuffered_write.c144 struct netfs_folio *finfo; in netfs_perform_write() local
203 finfo = netfs_folio_info(folio); in netfs_perform_write()
263 if (finfo) { in netfs_perform_write()
282 if (!finfo) { in netfs_perform_write()
296 finfo = kzalloc(sizeof(*finfo), GFP_KERNEL); in netfs_perform_write()
297 if (!finfo) { in netfs_perform_write()
302 finfo->netfs_group = netfs_get_group(netfs_group); in netfs_perform_write()
303 finfo->dirty_offset = offset; in netfs_perform_write()
304 finfo->dirty_len = copied; in netfs_perform_write()
305 folio_attach_private(folio, (void *)((unsigned long)finfo | in netfs_perform_write()
[all …]
H A Dmisc.c225 struct netfs_folio *finfo; in netfs_invalidate_folio() local
245 finfo = netfs_folio_info(folio); in netfs_invalidate_folio()
250 if (finfo) { in netfs_invalidate_folio()
252 unsigned int fstart = finfo->dirty_offset; in netfs_invalidate_folio()
253 unsigned int fend = fstart + finfo->dirty_len; in netfs_invalidate_folio()
269 finfo->dirty_len = fend - iend; in netfs_invalidate_folio()
270 finfo->dirty_offset = offset; in netfs_invalidate_folio()
278 finfo->dirty_len = offset - fstart; in netfs_invalidate_folio()
292 kfree(finfo); in netfs_invalidate_folio()
H A Dwrite_collect.c33 struct netfs_folio *finfo; in netfs_folio_written_back() local
37 if ((finfo = netfs_folio_info(folio))) { in netfs_folio_written_back()
43 fend = folio_pos(folio) + finfo->dirty_offset + finfo->dirty_len; in netfs_folio_written_back()
48 group = finfo->netfs_group; in netfs_folio_written_back()
50 kfree(finfo); in netfs_folio_written_back()
103 struct netfs_folio *finfo; in netfs_writeback_unlock_folios() local
115 finfo = netfs_folio_info(folio); in netfs_writeback_unlock_folios()
116 flen = finfo ? finfo->dirty_offset + finfo->dirty_len : fsize; in netfs_writeback_unlock_folios()
H A Dwrite_issue.c52 struct netfs_folio *finfo = NULL; in netfs_kill_dirty_pages() local
57 finfo = __netfs_folio_info(priv); in netfs_kill_dirty_pages()
58 if (finfo) { in netfs_kill_dirty_pages()
60 group = finfo->netfs_group; in netfs_kill_dirty_pages()
82 kfree(finfo); in netfs_kill_dirty_pages()
319 struct netfs_folio *finfo; in netfs_write_folio() local
349 finfo = netfs_folio_info(folio); in netfs_write_folio()
350 if (finfo) { in netfs_write_folio()
351 foff = finfo->dirty_offset; in netfs_write_folio()
352 flen = foff + finfo->dirty_len; in netfs_write_folio()
H A Dread_collect.c39 struct netfs_folio *finfo; in netfs_unlock_read_folio() local
46 finfo = netfs_folio_info(folio); in netfs_unlock_read_folio()
47 if (finfo) { in netfs_unlock_read_folio()
49 if (finfo->netfs_group) in netfs_unlock_read_folio()
50 folio_change_private(folio, finfo->netfs_group); in netfs_unlock_read_folio()
53 kfree(finfo); in netfs_unlock_read_folio()
/linux/tools/testing/selftests/mm/
H A Dkhugepaged.c74 static struct file_info finfo; variable
115 if (file_ops && finfo.type == VMA_FILE) in save_settings()
116 thp_set_read_ahead_path(finfo.dev_queue_read_ahead_path); in save_settings()
136 finfo.dir = dir; in get_finfo()
137 stat(finfo.dir, &path_stat); in get_finfo()
139 printf("%s: Not a directory (%s)\n", __func__, finfo.dir); in get_finfo()
142 if (snprintf(finfo.path, sizeof(finfo.path), "%s/" TEST_FILE, in get_finfo()
143 finfo.dir) >= sizeof(finfo.path)) { in get_finfo()
147 if (statfs(finfo.dir, &fs)) { in get_finfo()
151 finfo.type = fs.f_type == TMPFS_MAGIC ? VMA_SHMEM : VMA_FILE; in get_finfo()
[all …]
/linux/drivers/fpga/
H A Ddfl.c766 struct dfl_feature_info *finfo, *p; in build_info_commit_dev() local
810 list_for_each_entry_safe(finfo, p, &binfo->sub_features, node) { in build_info_commit_dev()
817 feature->id = finfo->fid; in build_info_commit_dev()
818 feature->revision = finfo->revision; in build_info_commit_dev()
819 feature->dfh_version = finfo->dfh_version; in build_info_commit_dev()
821 if (finfo->param_size) { in build_info_commit_dev()
823 finfo->params, finfo->param_size, in build_info_commit_dev()
828 feature->param_size = finfo->param_size; in build_info_commit_dev()
841 &finfo->mmio_res); in build_info_commit_dev()
846 fdev->resource[res_idx++] = finfo->mmio_res; in build_info_commit_dev()
[all …]
/linux/drivers/hid/usbhid/
H A Dhiddev.c601 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/drivers/gpu/drm/tidss/
H A Dtidss_plane.c31 const struct drm_format_info *finfo; in tidss_plane_atomic_check() local
72 finfo = drm_format_info(new_plane_state->fb->format->format); in tidss_plane_atomic_check()
74 if ((new_plane_state->src_x >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
77 __func__, (new_plane_state->src_x >> 16), finfo->hsub); in tidss_plane_atomic_check()
81 if ((new_plane_state->src_y >> 16) % finfo->vsub != 0) { in tidss_plane_atomic_check()
84 __func__, (new_plane_state->src_y >> 16), finfo->vsub); in tidss_plane_atomic_check()
88 if ((new_plane_state->src_w >> 16) % finfo->hsub != 0) { in tidss_plane_atomic_check()
92 finfo->hsub); in tidss_plane_atomic_check()
/linux/drivers/scsi/aic7xxx/aicasm/
H A Daicasm_symbol.c106 if (symbol->info.finfo != NULL) { in symbol_delete()
107 symlist_free(&symbol->info.finfo->symrefs); in symbol_delete()
108 free(symbol->info.finfo); in symbol_delete()
260 && (curnode->symbol->info.finfo->value > in symlist_add()
261 newnode->symbol->info.finfo->value)))) in symlist_add()
280 && (cursymbol->info.finfo->value > in symlist_add()
281 symbol->info.finfo->value)))) in symlist_add()
456 curnode->symbol->info.finfo->value, in aic_print_reg_dump_entry()
457 curnode->symbol->info.finfo->mask); in aic_print_reg_dump_entry()
583 regnode = SLIST_FIRST(&curnode->symbol->info.finfo->symrefs); in symtable_dump()
[all …]
H A Daicasm_gram.y710 $$.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 …]
/linux/drivers/net/ethernet/cavium/liquidio/
H A Dlio_vf_main.c802 struct octnet_buf_free_info *finfo; in free_netbuf() local
806 finfo = (struct octnet_buf_free_info *)buf; in free_netbuf()
807 skb = finfo->skb; in free_netbuf()
808 lio = finfo->lio; in free_netbuf()
810 dma_unmap_single(&lio->oct_dev->pci_dev->dev, finfo->dptr, skb->len, in free_netbuf()
822 struct octnet_buf_free_info *finfo; in free_netsgbuf() local
828 finfo = (struct octnet_buf_free_info *)buf; in free_netsgbuf()
829 skb = finfo->skb; in free_netsgbuf()
830 lio = finfo->lio; in free_netsgbuf()
831 g = finfo->g; in free_netsgbuf()
[all …]
H A Dlio_main.c1407 struct octnet_buf_free_info *finfo; in free_netbuf() local
1410 finfo = (struct octnet_buf_free_info *)buf; in free_netbuf()
1411 skb = finfo->skb; in free_netbuf()
1412 lio = finfo->lio; in free_netbuf()
1414 dma_unmap_single(&lio->oct_dev->pci_dev->dev, finfo->dptr, skb->len, in free_netbuf()
1426 struct octnet_buf_free_info *finfo; in free_netsgbuf() local
1432 finfo = (struct octnet_buf_free_info *)buf; in free_netsgbuf()
1433 skb = finfo->skb; in free_netsgbuf()
1434 lio = finfo->lio; in free_netsgbuf()
1435 g = finfo->g; in free_netsgbuf()
[all …]
/linux/drivers/gpu/drm/ingenic/
H A Dingenic-ipu.c329 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/drivers/media/usb/ttusb-dec/
H A Dttusb_dec.c562 struct filter_info *finfo; in ttusb_dec_process_filter() local
571 finfo = list_entry(item, struct filter_info, filter_info_list); in ttusb_dec_process_filter()
572 if (finfo->stream_id == sid) { in ttusb_dec_process_filter()
573 filter = finfo->filter; in ttusb_dec_process_filter()
1048 struct filter_info *finfo; in ttusb_dec_start_sec_feed() local
1064 if (!(finfo = kmalloc(sizeof(struct filter_info), in ttusb_dec_start_sec_feed()
1068 finfo->stream_id = c[1]; in ttusb_dec_start_sec_feed()
1069 finfo->filter = dvbdmxfeed->filter; in ttusb_dec_start_sec_feed()
1072 list_add_tail(&finfo->filter_info_list, in ttusb_dec_start_sec_feed()
1077 dvbdmxfeed->priv = finfo; in ttusb_dec_start_sec_feed()
[all …]
/linux/drivers/mtd/chips/
H A Djedec_probe.c2034 const struct amd_flash_info *finfo ) in jedec_match() argument
2051 mfr = (uint8_t)finfo->mfr_id; in jedec_match()
2052 id = (uint8_t)finfo->dev_id; in jedec_match()
2058 if (finfo->dev_id > 0xff) { in jedec_match()
2065 mfr = (uint16_t)finfo->mfr_id; in jedec_match()
2066 id = (uint16_t)finfo->dev_id; in jedec_match()
2069 mfr = (uint16_t)finfo->mfr_id; in jedec_match()
2070 id = (uint32_t)finfo->dev_id; in jedec_match()
2084 __func__, base, 1 << finfo->dev_size, base + (1 << finfo->dev_size) ); in jedec_match()
2085 if ( base + cfi_interleave(cfi) * ( 1 << finfo->dev_size ) > map->size ) { in jedec_match()
[all …]
/linux/drivers/net/wireless/realtek/rtw89/
H A Dcoex.c946 pmreg = &btc->fwinfo.rpt_fbtc_mregval.finfo; in _get_reg_status()
976 pmreg = &btc->fwinfo.rpt_fbtc_mregval.finfo; in _get_reg_status()
1186 union rtw89_btc_fbtc_btver *pver = &btc->fwinfo.rpt_fbtc_btver.finfo; in _update_bt_report()
1357 prpt = &pfwinfo->rpt_ctrl.finfo; in _chk_btc_report()
1359 pfinfo = &pfwinfo->rpt_ctrl.finfo.v1; in _chk_btc_report()
1360 pcinfo->req_len = sizeof(pfwinfo->rpt_ctrl.finfo.v1); in _chk_btc_report()
1362 pfinfo = &pfwinfo->rpt_ctrl.finfo.v4; in _chk_btc_report()
1363 pcinfo->req_len = sizeof(pfwinfo->rpt_ctrl.finfo.v4); in _chk_btc_report()
1365 pfinfo = &pfwinfo->rpt_ctrl.finfo.v5; in _chk_btc_report()
1366 pcinfo->req_len = sizeof(pfwinfo->rpt_ctrl.finfo.v5); in _chk_btc_report()
[all …]
/linux/include/linux/
H A Dnetfs.h117 struct netfs_folio *finfo; in netfs_folio_group() local
120 finfo = netfs_folio_info(folio); in netfs_folio_group()
121 if (finfo) in netfs_folio_group()
122 return finfo->netfs_group; in netfs_folio_group()
/linux/fs/nilfs2/
H A Drecovery.c328 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()
H A Dsegment.c512 struct nilfs_finfo *finfo; in nilfs_segctor_end_finfo() local
529 finfo = nilfs_segctor_map_segsum_entry(sci, &sci->sc_finfo_ptr, in nilfs_segctor_end_finfo()
530 sizeof(*finfo)); in nilfs_segctor_end_finfo()
531 finfo->fi_ino = cpu_to_le64(inode->i_ino); in nilfs_segctor_end_finfo()
532 finfo->fi_nblocks = cpu_to_le32(sci->sc_blk_cnt); in nilfs_segctor_end_finfo()
533 finfo->fi_ndatablk = cpu_to_le32(sci->sc_datablk_cnt); in nilfs_segctor_end_finfo()
534 finfo->fi_cno = cpu_to_le64(cno); in nilfs_segctor_end_finfo()
1599 struct nilfs_finfo *finfo = NULL; in nilfs_segctor_update_payload_blocknr() local
1615 if (!finfo) { in nilfs_segctor_update_payload_blocknr()
1616 finfo = nilfs_segctor_map_segsum_entry( in nilfs_segctor_update_payload_blocknr()
[all …]
/linux/drivers/gpu/drm/
H A Ddrm_fb_dma_helper.c125 const struct drm_format_info *finfo = state->fb->format; in drm_fb_dma_sync_non_coherent() local
133 for (i = 0; i < finfo->num_planes; i++) { in drm_fb_dma_sync_non_coherent()
/linux/drivers/hv/
H A Dhv_balloon.c142 } finfo; member
980 pg_start = dm->ha_wrk.ha_page_range.finfo.start_page; in hot_add_req()
981 pfn_cnt = dm->ha_wrk.ha_page_range.finfo.page_cnt; in hot_add_req()
983 rg_start = dm->ha_wrk.ha_region_range.finfo.start_page; in hot_add_req()
984 rg_sz = dm->ha_wrk.ha_region_range.finfo.page_cnt; in hot_add_req()
1183 int num_pages = range_array->finfo.page_cnt; in free_balloon_pages()
1184 __u64 start_frame = range_array->finfo.start_page; in free_balloon_pages()
1238 bl_resp->range_array[i].finfo.start_page = in alloc_balloon_pages()
1240 bl_resp->range_array[i].finfo.page_cnt = alloc_unit; in alloc_balloon_pages()
/linux/drivers/media/i2c/
H A Dds90ub913.c410 const struct ub913_format_info *finfo; in ub913_set_fmt() local
420 finfo = ub913_find_format(format->format.code); in ub913_set_fmt()
421 if (!finfo) { in ub913_set_fmt()
422 finfo = &ub913_formats[0]; in ub913_set_fmt()
423 format->format.code = finfo->incode; in ub913_set_fmt()
439 format->format.code = finfo->outcode; in ub913_set_fmt()
/linux/tools/bpf/bpftool/
H A Dcommon.c413 struct bpf_func_info finfo = {}; in get_prog_full_name() local
427 if (info.func_info_rec_size > sizeof(finfo)) in get_prog_full_name()
428 info.func_info_rec_size = sizeof(finfo); in get_prog_full_name()
429 info.func_info = ptr_to_u64(&finfo); in get_prog_full_name()
438 func_type = btf__type_by_id(prog_btf, finfo.type_id); in get_prog_full_name()

12