/linux-master/drivers/gpu/drm/i915/ |
H A D | i915_config.h | 15 u64 context);
|
/linux-master/include/linux/ |
H A D | dm-kcopyd.h | 65 void *context); 69 unsigned int flags, dm_kcopyd_notify_fn fn, void *context); 75 * It must not be called from interrupt context. 79 * It may be called from interrupt context. 83 dm_kcopyd_notify_fn fn, void *context); 88 unsigned int flags, dm_kcopyd_notify_fn fn, void *context);
|
/linux-master/arch/x86/include/asm/ |
H A D | init.h | 9 void *context; /* context for alloc_pgt_page */ member in struct:x86_mapping_info
|
/linux-master/drivers/gpu/drm/amd/display/dc/dml/dcn31/ |
H A D | dcn31_fpu.h | 38 void dcn31_update_soc_for_wm_a(struct dc *dc, struct dc_state *context); 39 void dcn315_update_soc_for_wm_a(struct dc *dc, struct dc_state *context); 42 struct dc *dc, struct dc_state *context, 56 struct dc_state *context,
|
/linux-master/drivers/acpi/ |
H A D | wakeup.c | 17 bool (*wakeup)(void *context); 18 void *context; member in struct:acpi_wakeup_handler 105 * @context: Context to pass to the handler when calling it 111 int acpi_register_wakeup_handler(int wake_irq, bool (*wakeup)(void *context), argument 112 void *context) 128 handler->context = context; 141 * @context: Context passed to acpi_register_wakeup_handler() 143 void acpi_unregister_wakeup_handler(bool (*wakeup)(void *context), argument 144 void *context) [all...] |
/linux-master/arch/sparc/include/asm/ |
H A D | mmu_context_64.h | 41 &mm->context.tsb_block[MM_TSB_BASE], 43 (mm->context.tsb_block[MM_TSB_HUGE].tsb ? 44 &mm->context.tsb_block[MM_TSB_HUGE] : 49 , __pa(&mm->context.tsb_descr[MM_TSB_BASE]), 64 /* Set MMU context in the actual hardware. */ 74 : "r" (CTX_HWBITS((__mm)->context)), \ 79 /* Switch the current MM context. */ 89 spin_lock_irqsave(&mm->context.lock, flags); 90 ctx_valid = CTX_VALID(mm->context); 101 * perform the secondary context loa [all...] |
/linux-master/include/sound/ |
H A D | tas2781-dsp.h | 172 void tasdevice_select_cfg_blk(void *context, int conf_no, 174 void tasdevice_config_info_remove(void *context); 175 void tasdevice_dsp_remove(void *context); 176 int tasdevice_dsp_parser(void *context); 177 int tasdevice_rca_parser(void *context, const struct firmware *fmw); 178 void tasdevice_dsp_remove(void *context); 179 void tasdevice_calbin_remove(void *context); 180 int tasdevice_select_tuningprm_cfg(void *context, int prm, 182 int tasdevice_prmg_load(void *context, int prm_no); 183 void tasdevice_tuning_switch(void *context, in [all...] |
/linux-master/sound/soc/codecs/ |
H A D | rl6347a.h | 28 int rl6347a_hw_write(void *context, unsigned int reg, unsigned int value); 29 int rl6347a_hw_read(void *context, unsigned int reg, unsigned int *value);
|
/linux-master/drivers/gpu/drm/amd/display/dc/clk_mgr/dce100/ |
H A D | dce_clk_mgr.h | 37 struct dc_state *context); 39 uint32_t dce_get_max_pixel_clock_for_all_paths(struct dc_state *context);
|
/linux-master/drivers/net/ethernet/mellanox/mlx5/core/lib/ |
H A D | hv.h | 16 int mlx5_hv_register_invalidate(struct mlx5_core_dev *dev, void *context, 17 void (*block_invalidate)(void *context,
|
/linux-master/arch/parisc/include/asm/ |
H A D | vdso.h | 12 #define VDSO64_SYMBOL(tsk, name) ((tsk)->mm->context.vdso_base + (vdso64_offset_##name)) 13 #define VDSO32_SYMBOL(tsk, name) ((tsk)->mm->context.vdso_base + (vdso32_offset_##name))
|
/linux-master/drivers/gpu/drm/amd/display/dc/resource/dce112/ |
H A D | dce112_resource.h | 42 struct dc_state *context, 47 struct dc_state *context,
|
/linux-master/tools/perf/scripts/perl/Perf-Trace-Util/ |
H A D | Context.c | 39 Perl_croak(aTHX_ "Usage: %s(%s)", "Perf::Trace::Context::common_pc", "context"); 42 struct scripting_context * context = INT2PTR(struct scripting_context *,SvIV(ST(0))); local 46 RETVAL = common_pc(context); 62 Perl_croak(aTHX_ "Usage: %s(%s)", "Perf::Trace::Context::common_flags", "context"); 65 struct scripting_context * context = INT2PTR(struct scripting_context *,SvIV(ST(0))); local 69 RETVAL = common_flags(context); 85 Perl_croak(aTHX_ "Usage: %s(%s)", "Perf::Trace::Context::common_lock_depth", "context"); 88 struct scripting_context * context = INT2PTR(struct scripting_context *,SvIV(ST(0))); local 92 RETVAL = common_lock_depth(context);
|
/linux-master/arch/riscv/include/asm/ |
H A D | kvm_vcpu_vector.h | 19 static __always_inline void __kvm_riscv_vector_save(struct kvm_cpu_context *context) argument 21 __riscv_v_vstate_save(&context->vector, context->vector.datap); 24 static __always_inline void __kvm_riscv_vector_restore(struct kvm_cpu_context *context) argument 26 __riscv_v_vstate_restore(&context->vector, context->vector.datap);
|
/linux-master/drivers/base/regmap/ |
H A D | regmap-ram.c | 19 static int regmap_ram_write(void *context, unsigned int reg, unsigned int val) argument 21 struct regmap_ram_data *data = context; 29 static int regmap_ram_read(void *context, unsigned int reg, unsigned int *val) argument 31 struct regmap_ram_data *data = context; 39 static void regmap_ram_free_context(void *context) argument 41 struct regmap_ram_data *data = context;
|
H A D | regmap-spmi.c | 16 static int regmap_spmi_base_read(void *context, argument 26 err = spmi_register_read(context, addr++, val++); 31 static int regmap_spmi_base_gather_write(void *context, argument 46 err = spmi_register_zero_write(context, *data); 56 err = spmi_register_write(context, addr, *data); 69 static int regmap_spmi_base_write(void *context, const void *data, argument 73 return regmap_spmi_base_gather_write(context, data, 1, data + 1, 105 static int regmap_spmi_ext_read(void *context, argument 124 err = spmi_ext_register_read(context, addr, val, len); 136 err = spmi_ext_register_readl(context, add 149 regmap_spmi_ext_gather_write(void *context, const void *reg, size_t reg_size, const void *val, size_t val_size) argument 189 regmap_spmi_ext_write(void *context, const void *data, size_t count) argument [all...] |
/linux-master/drivers/gpu/drm/amd/amdgpu/ |
H A D | amdgpu_psp_ta.c | 78 *pcontext = &psp->ras_context.context; 154 struct ta_context *context = NULL; local 179 /* Set TA context and functions */ 180 set_ta_context_funcs(psp, ta_type, &context); 192 if (!context->mem_context.shared_buf) { 193 ret = psp_ta_init_shared_buf(psp, &context->mem_context); 201 if (ret || context->resp_status) { 204 ret, context->resp_status); 210 /* Prepare TA context for TA initialization */ 211 context 253 struct ta_context *context = NULL; local 302 struct ta_context *context = NULL; local [all...] |
/linux-master/drivers/gpu/drm/i915/selftests/ |
H A D | i915_syncmap.c | 163 static int check_one(struct i915_syncmap **sync, u64 context, u32 seqno) argument 167 err = i915_syncmap_set(sync, context, seqno); 172 pr_err("Inserting first context=%llx did not return leaf (height=%d, prefix=%llx\n", 173 context, (*sync)->height, (*sync)->prefix); 178 pr_err("Inserting first context=%llx created branches!\n", 179 context); 193 if (!i915_syncmap_is_later(sync, context, seqno)) { 194 pr_err("Lookup of first context=%llx/seqno=%x failed!\n", 195 context, seqno); 217 u64 context local 238 check_leaf(struct i915_syncmap **sync, u64 context, u32 seqno) argument 297 u64 context = BIT_ULL(order); local 346 u64 context = step * BIT_ULL(order); local 363 u64 context = step * BIT_ULL(order); local 385 u64 context = step * BIT_ULL(order); local 414 u64 context = i915_prandom_u64_state(&prng) & ~MASK; local 469 u64 context = idx * BIT_ULL(order) + idx; local 562 u64 context = i915_prandom_u64_state(&prng); local 582 u64 context = i915_prandom_u64_state(&ctx); local [all...] |
/linux-master/security/selinux/ss/ |
H A D | sidtab.h | 4 * of security context structures indexed by SID value. 19 #include "context.h" 24 struct context context; member in struct:sidtab_entry 94 /* SID -> context string cache */ 103 /* Hash table for fast reverse context-to-sid lookups. */ 108 int sidtab_set_initial(struct sidtab *s, u32 sid, struct context *context); 112 static inline struct context *sidtab_search(struct sidtab *s, u32 sid) 116 return entry ? &entry->context [all...] |
H A D | mls.c | 30 * security context string representation of `context'. 32 int mls_compute_context_len(struct policydb *p, struct context *context) argument 44 u32 index_sens = context->range.level[l].sens; 50 e = &context->range.level[l].cat; 70 if (mls_level_eq(&context->range.level[0], 71 &context->range.level[1])) 82 * Write the security context string representation of 83 * the MLS fields of `context' int 86 mls_sid_to_context(struct policydb *p, struct context *context, char **scontext) argument 230 mls_context_to_sid(struct policydb *pol, char oldc, char *scontext, struct context *context, struct sidtab *s, u32 def_sid) argument 355 mls_from_string(struct policydb *p, char *str, struct context *context, gfp_t gfp_mask) argument 379 mls_range_set(struct context *context, struct mls_range *range) argument 553 mls_export_netlbl_lvl(struct policydb *p, struct context *context, struct netlbl_lsm_secattr *secattr) argument 574 mls_import_netlbl_lvl(struct policydb *p, struct context *context, struct netlbl_lsm_secattr *secattr) argument 595 mls_export_netlbl_cat(struct policydb *p, struct context *context, struct netlbl_lsm_secattr *secattr) argument 624 mls_import_netlbl_cat(struct policydb *p, struct context *context, struct netlbl_lsm_secattr *secattr) argument [all...] |
/linux-master/drivers/usb/image/ |
H A D | microtek.c | 78 * 20000515 Put transfer context and URB in mts_desc (john) 191 MTS_DEBUG("transfer = 0x%x context = 0x%x\n",(int)transfer,(int)context ); \ 192 MTS_DEBUG("status = 0x%x data-length = 0x%x sent = 0x%x\n",transfer->status,(int)context->data_length, (int)transfer->actual_length ); \ 193 mts_debug_dump(context->instance);\ 208 struct mts_transfer_context* context = (struct mts_transfer_context*)transfer->context; \ 370 /* Interrupt context! */ 372 /* Holding transfer->context->lock! */ 379 context [all...] |
/linux-master/drivers/gpu/drm/amd/display/dc/dml/dcn32/ |
H A D | dcn32_fpu.c | 183 static bool dcn32_apply_merge_split_flags_helper(struct dc *dc, struct dc_state *context, 276 struct dc_state *context, 282 struct vba_vars_st *vba = &context->bw_ctx.dml.vba; 284 enum clock_change_support temp_clock_change_support = vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb]; 290 vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb] = temp_clock_change_support; 291 context->bw_ctx.dml.soc.dram_clock_change_latency_us = 293 dcn32_internal_validate_bw(dc, context, pipes, &pipe_cnt, &vlevel, false); 297 dcn32_subvp_in_use(dc, context)) 298 vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb] = temp_clock_change_support; 300 if (vlevel < context 275 dcn32_find_dummy_latency_index_for_fw_based_mclk_switch(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt, int vlevel) argument 333 dcn32_helper_populate_phantom_dlg_params(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt) argument 466 dcn32_set_phantom_stream_timing(struct dc *dc, struct dc_state *context, struct pipe_ctx *ref_pipe, struct dc_stream_state *phantom_stream, display_e2e_pipe_params_st *pipes, unsigned int pipe_cnt, unsigned int dc_pipe_idx) argument 558 dcn32_get_num_free_pipes(struct dc *dc, struct dc_state *context) argument 599 dcn32_assign_subvp_pipe(struct dc *dc, struct dc_state *context, unsigned int *index) argument 678 dcn32_enough_pipes_for_subvp(struct dc *dc, struct dc_state *context) argument 724 subvp_subvp_schedulable(struct dc *dc, struct dc_state *context) argument 795 subvp_drr_schedulable(struct dc *dc, struct dc_state *context) argument 895 subvp_vblank_schedulable(struct dc *dc, struct dc_state *context) argument 982 subvp_subvp_admissable(struct dc *dc, struct dc_state *context) argument 1034 subvp_validate_static_schedulability(struct dc *dc, struct dc_state *context, int vlevel) argument 1090 assign_subvp_index(struct dc *dc, struct dc_state *context) argument 1164 init_pipe_slice_table_from_context( struct pipe_slice_table *table, struct dc_state *context) argument 1192 update_pipe_slice_table_with_split_flags( struct pipe_slice_table *table, struct dc *dc, struct dc_state *context, struct vba_vars_st *vba, int split[MAX_PIPES], bool merge[MAX_PIPES]) argument 1261 update_pipes_with_slice_table(struct dc *dc, struct dc_state *context, struct pipe_slice_table *table) argument 1279 update_pipes_with_split_flags(struct dc *dc, struct dc_state *context, struct vba_vars_st *vba, int split[MAX_PIPES], bool merge[MAX_PIPES]) argument 1294 should_apply_odm_power_optimization(struct dc *dc, struct dc_state *context, struct vba_vars_st *v, int *split, bool *merge) argument 1387 try_odm_power_optimization_and_revalidate( struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int *split, bool *merge, unsigned int *vlevel, int pipe_cnt) argument 1418 is_test_pattern_enabled( struct dc_state *context) argument 1431 dcn32_full_validate_bw_helper(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int *vlevel, int *split, bool *merge, int *pipe_cnt, bool *repopulate_pipes) argument 1592 is_dtbclk_required(struct dc *dc, struct dc_state *context) argument 1637 dcn32_calculate_dlg_params(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt, int vlevel) argument 1801 dcn32_find_split_pipe( struct dc *dc, struct dc_state *context, int old_index) argument 1929 dcn32_apply_merge_split_flags_helper( struct dc *dc, struct dc_state *context, bool *repopulate_pipes, int *split, bool *merge) argument 2130 dcn32_internal_validate_bw(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int *pipe_cnt_out, int *vlevel_out, bool fast_validate) argument 2292 dcn32_calculate_wm_and_dlg_fpu(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt, int vlevel) argument 3402 dcn32_allow_subvp_high_refresh_rate(struct dc *dc, struct dc_state *context, struct pipe_ctx *pipe) argument 3458 dcn32_determine_max_vratio_prefetch(struct dc *dc, struct dc_state *context) argument 3492 dcn32_assign_fpo_vactive_candidate(struct dc *dc, const struct dc_state *context, struct dc_stream_state **fpo_candidate_stream) argument 3528 dcn32_find_vactive_pipe(struct dc *dc, const struct dc_state *context, uint32_t vactive_margin_req_us) argument 3559 dcn32_override_min_req_memclk(struct dc *dc, struct dc_state *context) argument [all...] |
/linux-master/arch/m68k/include/asm/ |
H A D | mmu_context.h | 32 if (mm->context != NO_CONTEXT) 45 mm->context = ctx; 50 * Set up the context for a new address space. 52 #define init_new_context(tsk, mm) (((mm)->context = NO_CONTEXT), 0) 55 * We're finished using the context for an address space. 60 if (mm->context != NO_CONTEXT) { 61 clear_bit(mm->context, context_map); 62 mm->context = NO_CONTEXT; 67 static inline void set_context(mm_context_t context, pgd_t *pgd) argument 69 __asm__ __volatile__ ("movec %0,%%asid" : : "d" (context)); [all...] |
/linux-master/drivers/gpu/drm/amd/display/dc/hwss/ |
H A D | hw_sequencer_private.h | 77 void (*init_pipes)(struct dc *dc, struct dc_state *context); 78 void (*reset_hw_ctx_wrap)(struct dc *dc, struct dc_state *context); 103 struct dc_state *context, 138 void (*update_odm)(struct dc *dc, struct dc_state *context, 142 struct dc_state *context); 148 struct dc_state *context); 157 void (*PLAT_58856_wa)(struct dc_state *context, 161 struct dc_state *context); 162 void (*program_mall_pipe_config)(struct dc *dc, struct dc_state *context); 163 void (*update_force_pstate)(struct dc *dc, struct dc_state *context); [all...] |
/linux-master/drivers/gpu/drm/amd/display/dc/hwss/dcn35/ |
H A D | dcn35_hwseq.h | 34 void dcn35_update_odm(struct dc *dc, struct dc_state *context, struct pipe_ctx *pipe_ctx); 58 void dcn35_init_pipes(struct dc *dc, struct dc_state *context); 61 struct dc_state *context); 64 void dcn35_calc_blocks_to_gate(struct dc *dc, struct dc_state *context, 66 void dcn35_calc_blocks_to_ungate(struct dc *dc, struct dc_state *context, 77 struct dc_state *context); 81 struct dc_state *context);
|