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

1234567891011>>

/linux-master/include/linux/
H A Dobjpool.h63 typedef int (*objpool_init_obj_cb)(void *obj, void *context);
66 typedef int (*objpool_fini_cb)(struct objpool_head *head, void *context);
79 * @context: caller-provided context
91 void *context; member in struct:objpool_head
103 * @context: user context for object initialization callback
118 gfp_t gfp, void *context, objpool_init_obj_cb objinit,
/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/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/lib/kunit/
H A Dtry-catch.c28 try_catch->try(try_catch->context);
58 void kunit_try_catch_run(struct kunit_try_catch *try_catch, void *context) argument
65 try_catch->context = context;
72 try_catch->catch(try_catch->context);
96 try_catch->catch(try_catch->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/display/dc/dml2/
H A Ddml2_utils.h41 void dml2_copy_clocks_to_dc_state(struct dml2_dcn_clocks *out_clks, struct dc_state *context);
44 bool is_dtbclk_required(const struct dc *dc, struct dc_state *context);
59 * @context: To obtain res_ctx and read other information like stream ID etc.
61 * @out_hw_context : Handle to the new hardware context.
66 void dml2_dc_construct_pipes(struct dc_state *context, struct dml_mode_support_info_st *dml_mode_support_st,
72 * @context : dc_state.
79 bool dml2_predict_pipe_split(struct dc_state *context, display_pipe_params_st pipe, int index);
85 * @context : struct dc_state.
91 enum dc_status dml2_build_mapped_resource(const struct dc *dc, struct dc_state *context, struct dc_stream_state *stream);
96 * @context
[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...]
H A Dcontext.h3 * A security context is a set of security attributes
25 * A security context consists of an authenticated user
28 struct context { struct
34 char *str; /* string representation if context cannot be mapped. */
37 static inline void mls_context_init(struct context *c)
42 static inline int mls_context_cpy(struct context *dst,
43 const struct context *src)
63 static inline int mls_context_cpy_low(struct context *dst,
64 const struct context *src)
84 static inline int mls_context_cpy_high(struct context *ds
[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; \
376 /* Interrupt context! */
378 /* Holding transfer->context->lock! */
385 context
[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,
134 void (*update_odm)(struct dc *dc, struct dc_state *context,
138 struct dc_state *context);
144 struct dc_state *context);
153 void (*PLAT_58856_wa)(struct dc_state *context,
157 struct dc_state *context);
158 void (*program_mall_pipe_config)(struct dc *dc, struct dc_state *context);
159 void (*update_force_pstate)(struct dc *dc, struct dc_state *context);
[all...]
/linux-master/drivers/gpu/drm/amd/display/dc/dml/dcn32/
H A Ddcn32_fpu.c273 struct dc_state *context,
279 struct vba_vars_st *vba = &context->bw_ctx.dml.vba;
281 enum clock_change_support temp_clock_change_support = vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb];
287 vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb] = temp_clock_change_support;
288 context->bw_ctx.dml.soc.dram_clock_change_latency_us =
290 dcn32_internal_validate_bw(dc, context, pipes, &pipe_cnt, &vlevel, false);
294 dcn32_subvp_in_use(dc, context))
295 vba->DRAMClockChangeSupport[vlevel][context->bw_ctx.dml.vba.maxMpcComb] = temp_clock_change_support;
297 if (vlevel < context->bw_ctx.dml.vba.soc.num_states &&
322 * @context
272 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
330 dcn32_helper_populate_phantom_dlg_params(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt) argument
463 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
555 dcn32_get_num_free_pipes(struct dc *dc, struct dc_state *context) argument
596 dcn32_assign_subvp_pipe(struct dc *dc, struct dc_state *context, unsigned int *index) argument
675 dcn32_enough_pipes_for_subvp(struct dc *dc, struct dc_state *context) argument
721 subvp_subvp_schedulable(struct dc *dc, struct dc_state *context) argument
792 subvp_drr_schedulable(struct dc *dc, struct dc_state *context) argument
892 subvp_vblank_schedulable(struct dc *dc, struct dc_state *context) argument
979 subvp_subvp_admissable(struct dc *dc, struct dc_state *context) argument
1031 subvp_validate_static_schedulability(struct dc *dc, struct dc_state *context, int vlevel) argument
1087 assign_subvp_index(struct dc *dc, struct dc_state *context) argument
1161 init_pipe_slice_table_from_context( struct pipe_slice_table *table, struct dc_state *context) argument
1189 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
1258 update_pipes_with_slice_table(struct dc *dc, struct dc_state *context, struct pipe_slice_table *table) argument
1276 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
1291 should_apply_odm_power_optimization(struct dc *dc, struct dc_state *context, struct vba_vars_st *v, int *split, bool *merge) argument
1384 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
1415 is_test_pattern_enabled( struct dc_state *context) argument
1428 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) argument
1595 is_dtbclk_required(struct dc *dc, struct dc_state *context) argument
1640 dcn32_calculate_dlg_params(struct dc *dc, struct dc_state *context, display_e2e_pipe_params_st *pipes, int pipe_cnt, int vlevel) argument
1804 dcn32_find_split_pipe( struct dc *dc, struct dc_state *context, int old_index) argument
1932 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
2267 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
3377 dcn32_allow_subvp_high_refresh_rate(struct dc *dc, struct dc_state *context, struct pipe_ctx *pipe) argument
3433 dcn32_determine_max_vratio_prefetch(struct dc *dc, struct dc_state *context) argument
3467 dcn32_assign_fpo_vactive_candidate(struct dc *dc, const struct dc_state *context, struct dc_stream_state **fpo_candidate_stream) argument
3503 dcn32_find_vactive_pipe(struct dc *dc, const struct dc_state *context, uint32_t vactive_margin_req_us) argument
3534 dcn32_override_min_req_memclk(struct dc *dc, struct dc_state *context) argument
[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);
56 void dcn35_init_pipes(struct dc *dc, struct dc_state *context);
59 struct dc_state *context);
62 void dcn35_calc_blocks_to_gate(struct dc *dc, struct dc_state *context,
64 void dcn35_calc_blocks_to_ungate(struct dc *dc, struct dc_state *context,
75 struct dc_state *context);
79 struct dc_state *context);
/linux-master/drivers/comedi/drivers/
H A Dcomedi_8255.c36 unsigned long context; member in struct:subdev_8255_private
38 unsigned long context);
71 unsigned long context = spriv->context; local
79 s->state & 0xff, context);
82 (s->state >> 8) & 0xff, context);
85 (s->state >> 16) & 0xff, context);
88 v = spriv->io(dev, 0, I8255_DATA_A_REG, 0, context);
89 v |= (spriv->io(dev, 0, I8255_DATA_B_REG, 0, context) << 8);
90 v |= (spriv->io(dev, 0, I8255_DATA_C_REG, 0, context) << 1
101 unsigned long context = spriv->context; local
145 __subdev_8255_init(struct comedi_device *dev, struct comedi_subdevice *s, int (*io)(struct comedi_device *dev, int dir, int port, int data, unsigned long context), unsigned long context) argument
237 subdev_8255_cb_init(struct comedi_device *dev, struct comedi_subdevice *s, int (*io)(struct comedi_device *dev, int dir, int port, int data, unsigned long context), unsigned long context) argument
[all...]

Completed in 238 milliseconds

1234567891011>>