Searched refs:context (Results 76 - 100 of 2091) sorted by relevance

1234567891011>>

/linux-master/drivers/gpu/drm/i915/
H A Di915_config.h15 u64 context);
/linux-master/include/linux/
H A Ddm-kcopyd.h65 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 Dinit.h9 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 Ddcn31_fpu.h38 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 Dwakeup.c17 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 Dmmu_context_64.h41 &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 Dtas2781-dsp.h172 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 Drl6347a.h28 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 Ddce_clk_mgr.h37 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 Dhv.h16 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 Dvdso.h12 #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 Ddce112_resource.h42 struct dc_state *context,
47 struct dc_state *context,
/linux-master/tools/perf/scripts/perl/Perf-Trace-Util/
H A DContext.c39 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 Dkvm_vcpu_vector.h19 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 Dregmap-ram.c19 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 Dregmap-spmi.c16 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 Damdgpu_psp_ta.c78 *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 Di915_syncmap.c163 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 Dsidtab.h4 * 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 Dmls.c30 * 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 Dmicrotek.c78 * 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 Ddcn32_fpu.c183 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 Dmmu_context.h32 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 Dhw_sequencer_private.h77 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 Ddcn35_hwseq.h34 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);

Completed in 256 milliseconds

1234567891011>>