| /kernel/linux/linux-6.6/drivers/power/supply/ |
| H A D | qcom_battmgr.c | 182 } info; member
190 /* mWh or mAh, based on info->power_unit */
301 struct qcom_battmgr_info info; member
448 if (!battmgr->info.valid) { in qcom_battmgr_bat_sc8280xp_update()
452 battmgr->info.valid = true; in qcom_battmgr_bat_sc8280xp_update()
503 val->intval = battmgr->info.charge_type; in qcom_battmgr_bat_get_property()
509 val->intval = battmgr->info.present; in qcom_battmgr_bat_get_property()
512 val->intval = battmgr->info.technology; in qcom_battmgr_bat_get_property()
515 val->intval = battmgr->info.cycle_count; in qcom_battmgr_bat_get_property()
518 val->intval = battmgr->info in qcom_battmgr_bat_get_property()
[all...] |
| /kernel/linux/linux-6.6/drivers/accel/habanalabs/common/ |
| H A D | habanalabs_ioctl.c | 128 dev_err(hdev->dev, "Events info not supported\n"); in hw_events_info()
564 struct cpucp_hbm_row_info info = {0}; in dram_replaced_rows_info() local
571 rc = hl_fw_dram_replaced_row_get(hdev, &info); in dram_replaced_rows_info()
575 return copy_to_user(out, &info, min_t(size_t, max_size, sizeof(info))) ? -EFAULT : 0; in dram_replaced_rows_info()
580 struct hl_info_last_err_open_dev_time info = {0}; in last_err_open_dev_info() local
588 info.timestamp = ktime_to_ns(hdev->last_successful_open_ktime); in last_err_open_dev_info()
590 return copy_to_user(out, &info, min_t(size_t, max_size, sizeof(info))) ? -EFAULT : 0; in last_err_open_dev_info()
595 struct hl_info_cs_timeout_event info in cs_timeout_info() local
631 struct hl_info_undefined_opcode_event info = {0}; undefined_opcode_info() local
652 struct hl_info_dev_memalloc_page_sizes info = {0}; dev_mem_alloc_page_sizes_info() local
674 struct hl_info_sec_attest *info; sec_attest_info() local
839 struct hw_err_info *info; hw_err_info() local
861 struct fw_err_info *info; fw_err_info() local
[all...] |
| /kernel/linux/linux-5.10/drivers/video/fbdev/aty/ |
| H A D | mach64_accel.c | 67 void aty_init_engine(struct atyfb_par *par, struct fb_info *info) in aty_init_engine() argument
73 pitch_value = info->fix.line_length / (info->var.bits_per_pixel / 8); in aty_init_engine()
74 vxres = info->var.xres_virtual; in aty_init_engine()
76 if (info->var.bits_per_pixel == 24) { in aty_init_engine()
199 void atyfb_copyarea(struct fb_info *info, const struct fb_copyarea *area) in atyfb_copyarea() argument
201 struct atyfb_par *par = (struct atyfb_par *) info->par; in atyfb_copyarea()
210 cfb_copyarea(info, area); in atyfb_copyarea()
214 if (info->var.bits_per_pixel == 24) { in atyfb_copyarea()
234 if (info in atyfb_copyarea()
247 atyfb_fillrect(struct fb_info *info, const struct fb_fillrect *rect) atyfb_fillrect() argument
287 atyfb_imageblit(struct fb_info *info, const struct fb_image *image) atyfb_imageblit() argument
[all...] |
| /kernel/linux/linux-5.10/sound/core/seq/oss/ |
| H A D | seq_oss_event.c | 276 struct seq_oss_synthinfo *info; in note_on_event() local
278 info = snd_seq_oss_synth_info(dp, dev); in note_on_event()
279 if (!info) in note_on_event()
282 switch (info->arg.event_passing) { in note_on_event()
284 if (! info->ch || ch < 0 || ch >= info->nr_voices) { in note_on_event()
289 ch = array_index_nospec(ch, info->nr_voices); in note_on_event()
290 if (note == 255 && info->ch[ch].note >= 0) { in note_on_event()
297 if (info->ch[ch].vel) in note_on_event()
303 info in note_on_event()
337 struct seq_oss_synthinfo *info; note_off_event() local
[all...] |
| /kernel/linux/linux-6.6/drivers/video/fbdev/aty/ |
| H A D | mach64_accel.c | 67 void aty_init_engine(struct atyfb_par *par, struct fb_info *info) in aty_init_engine() argument
73 pitch_value = info->fix.line_length / (info->var.bits_per_pixel / 8); in aty_init_engine()
74 vxres = info->var.xres_virtual; in aty_init_engine()
76 if (info->var.bits_per_pixel == 24) { in aty_init_engine()
199 void atyfb_copyarea(struct fb_info *info, const struct fb_copyarea *area) in atyfb_copyarea() argument
201 struct atyfb_par *par = (struct atyfb_par *) info->par; in atyfb_copyarea()
210 cfb_copyarea(info, area); in atyfb_copyarea()
214 if (info->var.bits_per_pixel == 24) { in atyfb_copyarea()
234 if (info in atyfb_copyarea()
247 atyfb_fillrect(struct fb_info *info, const struct fb_fillrect *rect) atyfb_fillrect() argument
287 atyfb_imageblit(struct fb_info *info, const struct fb_image *image) atyfb_imageblit() argument
[all...] |
| /kernel/linux/linux-6.6/sound/core/seq/oss/ |
| H A D | seq_oss_event.c | 276 struct seq_oss_synthinfo *info; in note_on_event() local
278 info = snd_seq_oss_synth_info(dp, dev); in note_on_event()
279 if (!info) in note_on_event()
282 switch (info->arg.event_passing) { in note_on_event()
284 if (! info->ch || ch < 0 || ch >= info->nr_voices) { in note_on_event()
289 ch = array_index_nospec(ch, info->nr_voices); in note_on_event()
290 if (note == 255 && info->ch[ch].note >= 0) { in note_on_event()
297 if (info->ch[ch].vel) in note_on_event()
303 info in note_on_event()
337 struct seq_oss_synthinfo *info; note_off_event() local
[all...] |
| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| H A D | si_shaderlib_nir.c | 37 switch (nir->info.stage) { in create_shader_state()
92 b.shader->info.num_images = 2; in si_create_copy_image_cs()
97 b.shader->info.workgroup_size_variable = true; in si_create_copy_image_cs()
99 b.shader->info.cs.user_data_components_amd = 3; in si_create_copy_image_cs()
145 b.shader->info.workgroup_size[0] = 8; in si_create_dcc_retile_cs()
146 b.shader->info.workgroup_size[1] = 8; in si_create_dcc_retile_cs()
147 b.shader->info.workgroup_size[2] = 1; in si_create_dcc_retile_cs()
148 b.shader->info.cs.user_data_components_amd = 3; in si_create_dcc_retile_cs()
149 b.shader->info.num_ssbos = 1; in si_create_dcc_retile_cs()
170 ac_nir_dcc_addr_from_coord(&b, &sctx->screen->info, sur in si_create_dcc_retile_cs()
316 struct si_shader_info *info = &sctx->shader.vs.cso->info; si_create_passthrough_tcs() local
[all...] |
| /third_party/vk-gl-cts/framework/qphelper/ |
| H A D | qpCrashHandler.c | 49 /* Crash info write helper. */
62 /* Shared crash info. */
81 static void qpCrashInfo_init (qpCrashInfo* info) in qpCrashInfo_init() argument
83 info->type = QP_CRASHTYPE_LAST; in qpCrashInfo_init()
84 info->message = DE_NULL; in qpCrashInfo_init()
85 info->file = DE_NULL; in qpCrashInfo_init()
86 info->line = 0; in qpCrashInfo_init()
89 static void qpCrashInfo_set (qpCrashInfo* info, qpCrashType type, const char* message, const char* file, int line) in qpCrashInfo_set() argument
91 info->type = type; in qpCrashInfo_set()
92 info in qpCrashInfo_set()
97 qpCrashInfo_write(qpCrashInfo* info, qpWriteCrashInfoFunc writeInfo, void* userPtr) qpCrashInfo_write() argument
161 unhandledExceptionFilter(struct _EXCEPTION_POINTERS* info) unhandledExceptionFilter() argument
454 const SignalInfo* info = getSignalInfo(sigNum); signalHandler() local
[all...] |
| /kernel/linux/linux-5.10/scripts/mod/ |
| H A D | modpost.c | 318 static void *sym_get_data_by_offset(const struct elf_info *info, in sym_get_data_by_offset() argument
321 Elf_Shdr *sechdr = &info->sechdrs[secindex]; in sym_get_data_by_offset()
323 if (info->hdr->e_type != ET_REL) in sym_get_data_by_offset()
326 return (void *)info->hdr + sechdr->sh_offset + offset; in sym_get_data_by_offset()
329 static void *sym_get_data(const struct elf_info *info, const Elf_Sym *sym) in sym_get_data() argument
331 return sym_get_data_by_offset(info, get_secindex(info, sym), in sym_get_data()
335 static const char *sech_name(const struct elf_info *info, Elf_Shdr *sechdr) in sech_name() argument
337 return sym_get_data_by_offset(info, info in sech_name()
341 sec_name(const struct elf_info *info, int secindex) sec_name() argument
382 namespace_from_kstrtabns(const struct elf_info *info, const Elf_Sym *sym) namespace_from_kstrtabns() argument
474 parse_elf(struct elf_info *info, const char *filename) parse_elf() argument
637 parse_elf_finish(struct elf_info *info) parse_elf_finish() argument
642 ignore_undef_symbol(struct elf_info *info, const char *symname) ignore_undef_symbol() argument
671 handle_modversion(const struct module *mod, const struct elf_info *info, const Elf_Sym *sym, const char *symname) handle_modversion() argument
695 handle_symbol(struct module *mod, struct elf_info *info, const Elf_Sym *sym, const char *symname) handle_symbol() argument
772 get_next_modinfo(struct elf_info *info, const char *tag, char *prev) get_next_modinfo() argument
792 get_modinfo(struct elf_info *info, const char *tag) get_modinfo() argument
2028 struct elf_info info = { }; read_symbols() local
[all...] |
| /third_party/vk-gl-cts/external/vulkancts/modules/vulkan/memory/ |
| H A D | vktMemoryRequirementsTests.cpp | 81 VkBufferMemoryRequirementsInfo2 info = in getBufferMemoryRequirements2() local
94 vk.getBufferMemoryRequirements2(device, &info, &req2); in getBufferMemoryRequirements2()
136 VkImageMemoryRequirementsInfo2 info = in getImageMemoryRequirements2() local
149 vk.getImageMemoryRequirements2(device, &info, &req2); in getImageMemoryRequirements2()
157 VkDeviceImageMemoryRequirementsKHR info = in getDeviceImageMemoryRequirements() local
171 vk.getDeviceImageMemoryRequirements(device, &info, &req2); in getDeviceImageMemoryRequirements()
180 VkDeviceImageMemoryRequirementsKHR info = in getImageCreateInfoSparseMemoryRequirements() local
191 vk.getDeviceImageSparseMemoryRequirements(device, &info, &requirementsCount, DE_NULL); in getImageCreateInfoSparseMemoryRequirements()
202 vk.getDeviceImageSparseMemoryRequirements(device, &info, &requirementsCount, &requirements2[0]); in getImageCreateInfoSparseMemoryRequirements()
844 const VkImageCreateInfo& info);
1037 isImageSupported(const Context& context, const InstanceInterface& vki, const VkPhysicalDevice physDevice, const VkImageCreateInfo& info) isImageSupported() argument
1874 isMultiplaneImageSupported(const InstanceInterface& vki, const VkPhysicalDevice physicalDevice, const VkImageCreateInfo& info) isMultiplaneImageSupported() argument
2082 const VkDeviceImageMemoryRequirementsKHR info = testMultiplaneImages() local
2100 const VkImageMemoryRequirementsInfo2 info = testMultiplaneImages() local
[all...] |
| /kernel/linux/linux-5.10/mm/ |
| H A D | shmem.c | 142 struct shmem_inode_info *info, pgoff_t index);
218 struct shmem_inode_info *info = SHMEM_I(inode); in shmem_inode_acct_block() local
221 if (shmem_acct_block(info->flags, pages)) in shmem_inode_acct_block()
234 shmem_unacct_blocks(info->flags, pages); in shmem_inode_acct_block()
240 struct shmem_inode_info *info = SHMEM_I(inode); in shmem_inode_unacct_blocks() local
245 shmem_unacct_blocks(info->flags, pages); in shmem_inode_unacct_blocks()
357 * But normally info->alloced == inode->i_mapping->nrpages + info->swapped
358 * So mm freed is info->alloced - (inode->i_mapping->nrpages + info
364 struct shmem_inode_info *info = SHMEM_I(inode); shmem_recalc_inode() local
377 struct shmem_inode_info *info = SHMEM_I(inode); shmem_charge() local
397 struct shmem_inode_info *info = SHMEM_I(inode); shmem_uncharge() local
527 struct shmem_inode_info *info; shmem_unused_huge_shrink() local
820 struct shmem_inode_info *info = SHMEM_I(inode); shmem_swap_usage() local
908 struct shmem_inode_info *info = SHMEM_I(inode); shmem_undo_range() local
1072 struct shmem_inode_info *info = SHMEM_I(inode); shmem_getattr() local
1091 struct shmem_inode_info *info = SHMEM_I(inode); shmem_setattr() local
1157 struct shmem_inode_info *info = SHMEM_I(inode); shmem_evict_inode() local
1322 struct shmem_inode_info *info, *next; shmem_unuse() local
1366 struct shmem_inode_info *info; shmem_writepage() local
1507 shmem_pseudo_vma_init(struct vm_area_struct *vma, struct shmem_inode_info *info, pgoff_t index) shmem_pseudo_vma_init() argument
1523 shmem_swapin(swp_entry_t swap, gfp_t gfp, struct shmem_inode_info *info, pgoff_t index) shmem_swapin() argument
1539 shmem_alloc_hugepage(gfp_t gfp, struct shmem_inode_info *info, pgoff_t index) shmem_alloc_hugepage() argument
1563 shmem_alloc_page(gfp_t gfp, struct shmem_inode_info *info, pgoff_t index) shmem_alloc_page() argument
1580 struct shmem_inode_info *info = SHMEM_I(inode); shmem_alloc_and_acct_page() local
1625 shmem_replace_page(struct page **pagep, gfp_t gfp, struct shmem_inode_info *info, pgoff_t index) shmem_replace_page() argument
1704 struct shmem_inode_info *info = SHMEM_I(inode); shmem_swapin_page() local
1804 struct shmem_inode_info *info = SHMEM_I(inode); shmem_getpage_gfp() local
2236 struct shmem_inode_info *info = SHMEM_I(inode); shmem_lock() local
2263 struct shmem_inode_info *info = SHMEM_I(file_inode(file)); shmem_mmap() local
2287 struct shmem_inode_info *info; shmem_get_inode() local
2360 struct shmem_inode_info *info = SHMEM_I(inode); shmem_mfill_atomic_pte() local
2522 struct shmem_inode_info *info = SHMEM_I(inode); shmem_write_begin() local
2774 struct shmem_inode_info *info = SHMEM_I(inode); shmem_fallocate() local
3242 struct shmem_inode_info *info = SHMEM_I(inode); shmem_initxattrs() local
3275 struct shmem_inode_info *info = SHMEM_I(inode); shmem_xattr_handler_get() local
3286 struct shmem_inode_info *info = SHMEM_I(inode); shmem_xattr_handler_set() local
3316 struct shmem_inode_info *info = SHMEM_I(d_inode(dentry)); shmem_listxattr() local
3851 struct shmem_inode_info *info; shmem_alloc_inode() local
3873 struct shmem_inode_info *info = foo; shmem_init_inode() local
[all...] |
| /kernel/linux/linux-6.6/drivers/net/wireless/realtek/rtw89/ |
| H A D | debug.c | 2197 const struct rtw89_mac_dbg_port_info *info; in rtw89_debug_mac_dbg_port_sel() local
2205 info = &dbg_port_ptcl_c0; in rtw89_debug_mac_dbg_port_sel()
2212 info = &dbg_port_ptcl_c1; in rtw89_debug_mac_dbg_port_sel()
2219 info = &dbg_port_sch_c0; in rtw89_debug_mac_dbg_port_sel()
2226 info = &dbg_port_sch_c1; in rtw89_debug_mac_dbg_port_sel()
2233 info = &dbg_port_tmac_c0; in rtw89_debug_mac_dbg_port_sel()
2250 info = &dbg_port_tmac_c1; in rtw89_debug_mac_dbg_port_sel()
2267 info = &dbg_port_rmac_c0; in rtw89_debug_mac_dbg_port_sel()
2289 info = &dbg_port_rmac_c1; in rtw89_debug_mac_dbg_port_sel()
2311 info in rtw89_debug_mac_dbg_port_sel()
2800 const struct rtw89_mac_dbg_port_info *info; rtw89_debug_mac_dbg_port_dump() local
3367 const struct rtw89_rx_rate_cnt_info *info; rtw89_debug_priv_phy_info_get() local
3428 struct rtw89_pktofld_info *info; rtw89_dump_pkt_offload() local
[all...] |
| /kernel/linux/linux-5.10/drivers/video/fbdev/geode/ |
| H A D | lxfb_ops.c | 160 static void lx_set_clock(struct fb_info *info) in lx_set_clock() argument
165 freq = (unsigned int) (1000000000 / info->var.pixclock); in lx_set_clock()
180 static void lx_graphics_disable(struct fb_info *info) in lx_graphics_disable() argument
182 struct lxfb_par *par = info->par; in lx_graphics_disable()
245 static void lx_graphics_enable(struct fb_info *info) in lx_graphics_enable() argument
247 struct lxfb_par *par = info->par; in lx_graphics_enable()
263 if (info->var.sync & FB_SYNC_HOR_HIGH_ACT) in lx_graphics_enable()
266 if (info->var.sync & FB_SYNC_VERT_HIGH_ACT) in lx_graphics_enable()
275 if (!(info->var.sync & FB_SYNC_HOR_HIGH_ACT)) in lx_graphics_enable()
278 if (!(info in lx_graphics_enable()
341 lx_set_mode(struct fb_info *info) lx_set_mode() argument
505 lx_set_palette_reg(struct fb_info *info, unsigned regno, unsigned red, unsigned green, unsigned blue) lx_set_palette_reg() argument
521 lx_blank_display(struct fb_info *info, int blank_mode) lx_blank_display() argument
812 lx_powerdown(struct fb_info *info) lx_powerdown() argument
826 lx_powerup(struct fb_info *info) lx_powerup() argument
[all...] |
| /kernel/linux/linux-5.10/net/mac80211/ |
| H A D | rate.c | 301 struct ieee80211_tx_info *info = IEEE80211_SKB_CB(skb); in rc_no_data_or_no_ack_use_min() local
306 return (info->flags & (IEEE80211_TX_CTL_NO_ACK | in rc_no_data_or_no_ack_use_min()
344 struct ieee80211_tx_info *info, in __rate_control_send_low()
352 info->control.rates[0].flags |= IEEE80211_TX_RC_S1G_MCS; in __rate_control_send_low()
353 info->control.rates[0].idx = 0; in __rate_control_send_low()
358 (info->flags & IEEE80211_TX_CTL_NO_CCK_RATE)) in __rate_control_send_low()
361 info->control.rates[0].idx = 0; in __rate_control_send_low()
372 info->control.rates[0].idx = i; in __rate_control_send_low()
382 info->control.rates[0].count = in __rate_control_send_low()
383 (info in __rate_control_send_low()
341 __rate_control_send_low(struct ieee80211_hw *hw, struct ieee80211_supported_band *sband, struct ieee80211_sta *sta, struct ieee80211_tx_info *info, u32 rate_mask) __rate_control_send_low() argument
393 struct ieee80211_tx_info *info = IEEE80211_SKB_CB(txrc->skb); rate_control_send_low() local
610 rate_fixup_ratelist(struct ieee80211_vif *vif, struct ieee80211_supported_band *sband, struct ieee80211_tx_info *info, struct ieee80211_tx_rate *rates, int max_rates) rate_fixup_ratelist() argument
713 rate_control_fill_sta_table(struct ieee80211_sta *sta, struct ieee80211_tx_info *info, struct ieee80211_tx_rate *rates, int max_rates) rate_control_fill_sta_table() argument
874 struct ieee80211_tx_info *info = IEEE80211_SKB_CB(skb); ieee80211_get_tx_rates() local
904 struct ieee80211_tx_info *info = IEEE80211_SKB_CB(txrc->skb); rate_control_get_rate() local
[all...] |
| /kernel/linux/linux-6.6/drivers/video/fbdev/geode/ |
| H A D | lxfb_ops.c | 160 static void lx_set_clock(struct fb_info *info) in lx_set_clock() argument
165 freq = (unsigned int) (1000000000 / info->var.pixclock); in lx_set_clock()
180 static void lx_graphics_disable(struct fb_info *info) in lx_graphics_disable() argument
182 struct lxfb_par *par = info->par; in lx_graphics_disable()
245 static void lx_graphics_enable(struct fb_info *info) in lx_graphics_enable() argument
247 struct lxfb_par *par = info->par; in lx_graphics_enable()
263 if (info->var.sync & FB_SYNC_HOR_HIGH_ACT) in lx_graphics_enable()
266 if (info->var.sync & FB_SYNC_VERT_HIGH_ACT) in lx_graphics_enable()
275 if (!(info->var.sync & FB_SYNC_HOR_HIGH_ACT)) in lx_graphics_enable()
278 if (!(info in lx_graphics_enable()
341 lx_set_mode(struct fb_info *info) lx_set_mode() argument
505 lx_set_palette_reg(struct fb_info *info, unsigned regno, unsigned red, unsigned green, unsigned blue) lx_set_palette_reg() argument
521 lx_blank_display(struct fb_info *info, int blank_mode) lx_blank_display() argument
813 lx_powerdown(struct fb_info *info) lx_powerdown() argument
827 lx_powerup(struct fb_info *info) lx_powerup() argument
[all...] |
| /kernel/linux/linux-5.10/arch/x86/mm/ |
| H A D | tlb.c | 27 # define __flush_tlb_others(msk, info) native_flush_tlb_others(msk, info)
773 static void flush_tlb_func_local(const void *info, enum tlb_flush_reason reason) in flush_tlb_func_local() argument
775 const struct flush_tlb_info *f = info; in flush_tlb_func_local()
780 static void flush_tlb_func_remote(void *info) in flush_tlb_func_remote() argument
782 const struct flush_tlb_info *f = info; in flush_tlb_func_remote()
799 const struct flush_tlb_info *info) in native_flush_tlb_others()
802 if (info->end == TLB_FLUSH_ALL) in native_flush_tlb_others()
806 (info->end - info in native_flush_tlb_others()
798 native_flush_tlb_others(const struct cpumask *cpumask, const struct flush_tlb_info *info) native_flush_tlb_others() argument
826 flush_tlb_others(const struct cpumask *cpumask, const struct flush_tlb_info *info) flush_tlb_others() argument
855 struct flush_tlb_info *info = this_cpu_ptr(&flush_tlb_info); get_flush_tlb_info() local
889 struct flush_tlb_info *info; flush_tlb_mm_range() local
916 flush_tlb_others(mm_cpumask(mm), info); flush_tlb_mm_range() local
923 do_flush_tlb_all(void *info) do_flush_tlb_all() argument
935 do_kernel_range_flush(void *info) do_kernel_range_flush() argument
952 struct flush_tlb_info *info; flush_tlb_kernel_range() local
[all...] |
| /kernel/linux/linux-5.10/drivers/soc/ti/ |
| H A D | knav_qmss_acc.c | 83 struct knav_acc_info *info; in knav_acc_int_handler() local
91 info = &range->acc_info; in knav_acc_int_handler()
123 dma_sync_single_for_cpu(kdev->dev, list_dma, info->list_size, in knav_acc_int_handler()
126 for (list = list_cpu; list < list_cpu + (info->list_size / sizeof(u32)); in knav_acc_int_handler()
178 memset(list_cpu, 0, info->list_size); in knav_acc_int_handler()
179 dma_sync_single_for_device(kdev->dev, list_dma, info->list_size, in knav_acc_int_handler()
305 struct knav_acc_info *info = &range->acc_info; in knav_acc_setup_cmd() local
324 cmd->queue_num = info->list_entries << 16; in knav_acc_setup_cmd()
330 cmd->timer_config |= info->pacing_mode << 16; in knav_acc_setup_cmd()
331 cmd->timer_config |= info in knav_acc_setup_cmd()
431 struct knav_acc_info *info; knav_acc_free_range() local
477 struct knav_acc_info *info; knav_init_acc_range() local
[all...] |
| /kernel/linux/linux-5.10/kernel/ |
| H A D | taskstats.c | 65 static int prepare_reply(struct genl_info *info, u8 cmd, struct sk_buff **skbp, in prepare_reply() argument
78 if (!info) { in prepare_reply()
83 reply = genlmsg_put_reply(skb, info, &family, 0, cmd); in prepare_reply()
96 static int send_reply(struct sk_buff *skb, struct genl_info *info) in send_reply() argument
103 return genlmsg_reply(skb, info); in send_reply()
385 static int cgroupstats_user_cmd(struct sk_buff *skb, struct genl_info *info) in cgroupstats_user_cmd() argument
395 na = info->attrs[CGROUPSTATS_CMD_ATTR_FD]; in cgroupstats_user_cmd()
399 fd = nla_get_u32(info->attrs[CGROUPSTATS_CMD_ATTR_FD]); in cgroupstats_user_cmd()
406 rc = prepare_reply(info, CGROUPSTATS_CMD_NEW, &rep_skb, in cgroupstats_user_cmd()
428 rc = send_reply(rep_skb, info); in cgroupstats_user_cmd()
435 cmd_attr_register_cpumask(struct genl_info *info) cmd_attr_register_cpumask() argument
451 cmd_attr_deregister_cpumask(struct genl_info *info) cmd_attr_deregister_cpumask() argument
478 cmd_attr_pid(struct genl_info *info) cmd_attr_pid() argument
507 cmd_attr_tgid(struct genl_info *info) cmd_attr_tgid() argument
536 taskstats_user_cmd(struct sk_buff *skb, struct genl_info *info) taskstats_user_cmd() argument
[all...] |
| /kernel/linux/linux-6.6/drivers/soc/ti/ |
| H A D | knav_qmss_acc.c | 83 struct knav_acc_info *info; in knav_acc_int_handler() local
91 info = &range->acc_info; in knav_acc_int_handler()
123 dma_sync_single_for_cpu(kdev->dev, list_dma, info->list_size, in knav_acc_int_handler()
126 for (list = list_cpu; list < list_cpu + (info->list_size / sizeof(u32)); in knav_acc_int_handler()
178 memset(list_cpu, 0, info->list_size); in knav_acc_int_handler()
179 dma_sync_single_for_device(kdev->dev, list_dma, info->list_size, in knav_acc_int_handler()
305 struct knav_acc_info *info = &range->acc_info; in knav_acc_setup_cmd() local
324 cmd->queue_num = info->list_entries << 16; in knav_acc_setup_cmd()
330 cmd->timer_config |= info->pacing_mode << 16; in knav_acc_setup_cmd()
331 cmd->timer_config |= info in knav_acc_setup_cmd()
431 struct knav_acc_info *info; knav_acc_free_range() local
477 struct knav_acc_info *info; knav_init_acc_range() local
[all...] |
| /kernel/linux/linux-6.6/drivers/platform/x86/intel/ |
| H A D | sdsi.c | 159 static int sdsi_mbox_cmd_read(struct sdsi_priv *priv, struct sdsi_mbox_info *info, in sdsi_mbox_cmd_read() argument
173 FIELD_PREP(CTRL_PACKET_SIZE, info->size); in sdsi_mbox_cmd_read()
180 void *buf = info->buffer + (SDSI_SIZE_MAILBOX * loop); in sdsi_mbox_cmd_read()
238 static int sdsi_mbox_cmd_write(struct sdsi_priv *priv, struct sdsi_mbox_info *info) in sdsi_mbox_cmd_write() argument
247 sdsi_memcpy64_toio(priv->mbox_addr + SDSI_SIZE_CMD, info->payload + 1, in sdsi_mbox_cmd_write()
248 info->size - SDSI_SIZE_CMD); in sdsi_mbox_cmd_write()
255 FIELD_PREP(CTRL_PACKET_SIZE, info->size); in sdsi_mbox_cmd_write()
274 static int sdsi_mbox_acquire(struct sdsi_priv *priv, struct sdsi_mbox_info *info) in sdsi_mbox_acquire() argument
295 writeq(info->payload[0], priv->mbox_addr); in sdsi_mbox_acquire()
315 static int sdsi_mbox_write(struct sdsi_priv *priv, struct sdsi_mbox_info *info) in sdsi_mbox_write() argument
328 sdsi_mbox_read(struct sdsi_priv *priv, struct sdsi_mbox_info *info, size_t *data_size) sdsi_mbox_read() argument
344 struct sdsi_mbox_info info; sdsi_provision() local
410 struct sdsi_mbox_info info; certificate_read() local
[all...] |
| /kernel/linux/linux-6.6/net/netfilter/ |
| H A D | nfnetlink_cttimeout.c | 99 const struct nfnl_info *info, in cttimeout_new_timeout()
102 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_new_timeout()
124 if (info->nlh->nlmsg_flags & NLM_F_EXCL) in cttimeout_new_timeout()
132 if (info->nlh->nlmsg_flags & NLM_F_REPLACE) { in cttimeout_new_timeout()
142 info->net, in cttimeout_new_timeout()
165 info->net, cda[CTA_TIMEOUT_DATA]); in cttimeout_new_timeout()
264 const struct nfnl_info *info, in cttimeout_get_timeout()
267 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_get_timeout()
272 if (info->nlh->nlmsg_flags & NLM_F_DUMP) { in cttimeout_get_timeout()
276 return netlink_dump_start(info in cttimeout_get_timeout()
98 cttimeout_new_timeout(struct sk_buff *skb, const struct nfnl_info *info, const struct nlattr * const cda[]) cttimeout_new_timeout() argument
263 cttimeout_get_timeout(struct sk_buff *skb, const struct nfnl_info *info, const struct nlattr * const cda[]) cttimeout_get_timeout() argument
330 cttimeout_del_timeout(struct sk_buff *skb, const struct nfnl_info *info, const struct nlattr * const cda[]) cttimeout_del_timeout() argument
361 cttimeout_default_set(struct sk_buff *skb, const struct nfnl_info *info, const struct nlattr * const cda[]) cttimeout_default_set() argument
433 cttimeout_default_get(struct sk_buff *skb, const struct nfnl_info *info, const struct nlattr * const cda[]) cttimeout_default_get() argument
[all...] |
| /kernel/linux/linux-6.6/kernel/ |
| H A D | taskstats.c | 66 static int prepare_reply(struct genl_info *info, u8 cmd, struct sk_buff **skbp, in prepare_reply() argument
79 if (!info) { in prepare_reply()
84 reply = genlmsg_put_reply(skb, info, &family, 0, cmd); in prepare_reply()
97 static int send_reply(struct sk_buff *skb, struct genl_info *info) in send_reply() argument
104 return genlmsg_reply(skb, info); in send_reply()
197 /* add executable info */ in fill_stats()
407 static int cgroupstats_user_cmd(struct sk_buff *skb, struct genl_info *info) in cgroupstats_user_cmd() argument
417 na = info->attrs[CGROUPSTATS_CMD_ATTR_FD]; in cgroupstats_user_cmd()
421 fd = nla_get_u32(info->attrs[CGROUPSTATS_CMD_ATTR_FD]); in cgroupstats_user_cmd()
428 rc = prepare_reply(info, CGROUPSTATS_CMD_NE in cgroupstats_user_cmd()
457 cmd_attr_register_cpumask(struct genl_info *info) cmd_attr_register_cpumask() argument
473 cmd_attr_deregister_cpumask(struct genl_info *info) cmd_attr_deregister_cpumask() argument
500 cmd_attr_pid(struct genl_info *info) cmd_attr_pid() argument
529 cmd_attr_tgid(struct genl_info *info) cmd_attr_tgid() argument
558 taskstats_user_cmd(struct sk_buff *skb, struct genl_info *info) taskstats_user_cmd() argument
[all...] |
| /third_party/mesa3d/src/gallium/drivers/nouveau/nvc0/ |
| H A D | nvc0_compute.c | 384 const struct pipe_grid_info *info) in nvc0_compute_upload_input()
403 PUSH_DATAp(push, info->input, cp->parm_size / 4); in nvc0_compute_upload_input()
416 PUSH_DATA (push, info->work_dim); in nvc0_compute_upload_input()
423 nvc0_launch_grid(struct pipe_context *pipe, const struct pipe_grid_info *info) in nvc0_launch_grid() argument
437 nvc0_compute_upload_input(nvc0, info); in nvc0_launch_grid()
449 PUSH_DATA (push, info->block[0] * info->block[1] * info->block[2]); in nvc0_launch_grid()
464 PUSH_DATA (push, (info->block[1] << 16) | info in nvc0_launch_grid()
383 nvc0_compute_upload_input(struct nvc0_context *nvc0, const struct pipe_grid_info *info) nvc0_compute_upload_input() argument
508 nvc0_compute_update_indirect_invocations(struct nvc0_context *nvc0, const struct pipe_grid_info *info) nvc0_compute_update_indirect_invocations() argument
526 nvc0_update_compute_invocations_counter(struct nvc0_context *nvc0, const struct pipe_grid_info *info) nvc0_update_compute_invocations_counter() argument
[all...] |
| /kernel/linux/linux-5.10/drivers/vfio/pci/ |
| H A D | vfio_pci.c | 698 struct vfio_pci_group_info *info = data; in vfio_pci_validate_devs() local
708 for (i = 0; i < info->count; i++) in vfio_pci_validate_devs()
709 if (info->groups[i].id == id) in vfio_pci_validate_devs()
714 return (i == info->count) ? -EINVAL : 0; in vfio_pci_validate_devs()
807 struct vfio_device_info info; in vfio_pci_ioctl() local
816 if (copy_from_user(&info, (void __user *)arg, minsz)) in vfio_pci_ioctl()
819 if (info.argsz < minsz) in vfio_pci_ioctl()
822 if (info.argsz >= capsz) { in vfio_pci_ioctl()
824 info.cap_offset = 0; in vfio_pci_ioctl()
827 info in vfio_pci_ioctl()
867 struct vfio_region_info info; vfio_pci_ioctl() local
1011 struct vfio_irq_info info; vfio_pci_ioctl() local
1170 struct vfio_pci_group_info info; vfio_pci_ioctl() local
[all...] |
| /kernel/linux/linux-5.10/drivers/acpi/acpica/ |
| H A D | utpredef.c | 38 * cases where a package info entry follows a method name that
50 * (next entry contains the package info) in acpi_ut_get_next_predefined_method()
52 if ((this_name->info.expected_btypes & ACPI_RTYPE_PACKAGE) && in acpi_ut_get_next_predefined_method()
53 (this_name->info.expected_btypes != ACPI_RTYPE_ALL)) { in acpi_ut_get_next_predefined_method()
83 /* Search info table for a predefined method/object name */ in acpi_ut_match_predefined_method()
86 while (this_name->info.name[0]) { in acpi_ut_match_predefined_method()
87 if (ACPI_COMPARE_NAMESEG(name, this_name->info.name)) { in acpi_ut_match_predefined_method()
200 /* Search info table for a predefined method/object name */ in acpi_ut_match_resource_name()
203 while (this_name->info.name[0]) { in acpi_ut_match_resource_name()
204 if (ACPI_COMPARE_NAMESEG(name, this_name->info in acpi_ut_match_resource_name()
[all...] |