/linux-master/include/linux/ |
H A D | objpool.h | 63 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 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/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/lib/kunit/ |
H A D | try-catch.c | 28 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 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/display/dc/dml2/ |
H A D | dml2_utils.h | 41 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 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...] |
H A D | context.h | 3 * 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 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; \ 376 /* Interrupt context! */ 378 /* Holding transfer->context->lock! */ 385 context [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, 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 D | dcn32_fpu.c | 273 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 D | dcn35_hwseq.h | 34 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 D | comedi_8255.c | 36 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...] |