| /linux/drivers/gpu/drm/ |
| H A D | drm_fourcc.c | 40 uint32_t drm_mode_legacy_fb_format(uint32_t bpp, uint32_t depth) in drm_mode_legacy_fb_format() argument
46 if (depth == 1) in drm_mode_legacy_fb_format()
51 if (depth == 2) in drm_mode_legacy_fb_format()
56 if (depth == 4) in drm_mode_legacy_fb_format()
61 if (depth == 8) in drm_mode_legacy_fb_format()
66 switch (depth) { in drm_mode_legacy_fb_format()
79 if (depth == 24) in drm_mode_legacy_fb_format()
84 switch (depth) { in drm_mode_legacy_fb_format()
119 uint32_t bpp, uint32_t depth) in drm_driver_legacy_fb_format() argument
121 uint32_t fmt = drm_mode_legacy_fb_format(bpp, depth); in drm_driver_legacy_fb_format()
[all …]
|
| /linux/lib/ |
| H A D | sbitmap.c | 14 unsigned depth = sb->depth; in init_alloc_hint() local
20 if (depth && !sb->round_robin) { in init_alloc_hint()
24 *per_cpu_ptr(sb->alloc_hint, i) = get_random_u32_below(depth); in init_alloc_hint()
30 unsigned int depth) in update_alloc_hint_before_get() argument
35 if (unlikely(hint >= depth)) { in update_alloc_hint_before_get()
36 hint = depth ? get_random_u32_below(depth) : 0; in update_alloc_hint_before_get()
44 unsigned int depth, in update_alloc_hint_after_get() argument
54 if (hint >= depth - 1) in update_alloc_hint_after_get()
64 unsigned int depth, unsigned int alloc_hint, bool wrap) in sbitmap_deferred_clear() argument
71 if (depth == 0) in sbitmap_deferred_clear()
[all …]
|
| /linux/fs/quota/ |
| H A D | quota_tree.c | 32 static int __get_index(struct qtree_mem_dqinfo *info, qid_t id, int depth) in __get_index() argument
36 depth = info->dqi_qtree_depth - depth - 1; in __get_index()
37 while (depth--) in __get_index()
42 static int get_index(struct qtree_mem_dqinfo *info, struct kqid qid, int depth) in get_index() argument
46 return __get_index(info, id, depth); in get_index()
336 uint *blks, int depth) in do_insert_tree() argument
346 if (!blks[depth]) { in do_insert_tree()
350 for (i = 0; i < depth; i++) in do_insert_tree()
358 blks[depth] = ret; in do_insert_tree()
362 ret = read_blk(info, blks[depth], buf); in do_insert_tree()
[all …]
|
| /linux/fs/ext4/ |
| H A D | extents.c | 113 int depth, i; in ext4_ext_drop_refs() local
117 depth = path->p_depth; in ext4_ext_drop_refs()
118 for (i = 0; i <= depth; i++, path++) in ext4_ext_drop_refs()
220 int depth = path->p_depth; in ext4_ext_find_goal() local
240 ex = path[depth].p_ext; in ext4_ext_find_goal()
253 if (path[depth].p_bh) in ext4_ext_find_goal()
254 return path[depth].p_bh->b_blocknr; in ext4_ext_find_goal()
345 ext4_ext_max_entries(struct inode *inode, int depth) in ext4_ext_max_entries() argument
349 if (depth == ext_depth(inode)) { in ext4_ext_max_entries()
350 if (depth == 0) in ext4_ext_max_entries()
[all …]
|
| /linux/arch/powerpc/platforms/powernv/ |
| H A D | opal-tracepoints.c | 50 unsigned int *depth; in __trace_opal_entry() local
54 depth = this_cpu_ptr(&opal_trace_depth); in __trace_opal_entry()
56 if (*depth) in __trace_opal_entry()
59 (*depth)++; in __trace_opal_entry()
62 (*depth)--; in __trace_opal_entry()
71 unsigned int *depth; in __trace_opal_exit() local
75 depth = this_cpu_ptr(&opal_trace_depth); in __trace_opal_exit()
77 if (*depth) in __trace_opal_exit()
80 (*depth)++; in __trace_opal_exit()
83 (*depth)--; in __trace_opal_exit()
|
| /linux/drivers/media/platform/mediatek/mdp3/ |
| H A D | mdp_cfg_data.c | 824 .depth = { 8 },
831 .depth = { 16 },
838 .depth = { 16 },
845 .depth = { 24 },
852 .depth = { 24 },
859 .depth = { 32 },
866 .depth = { 32 },
873 .depth = { 16 },
881 .depth = { 16 },
889 .depth = { 16 },
[all …]
|
| /linux/kernel/irq/ |
| H A D | irq_test.c | 76 KUNIT_EXPECT_EQ(test, desc->depth, 0); in irq_disable_depth_test()
79 KUNIT_EXPECT_EQ(test, desc->depth, 1); in irq_disable_depth_test()
82 KUNIT_EXPECT_EQ(test, desc->depth, 0); in irq_disable_depth_test()
100 KUNIT_EXPECT_EQ(test, desc->depth, 0); in irq_free_disabled_test()
103 KUNIT_EXPECT_EQ(test, desc->depth, 1); in irq_free_disabled_test()
106 KUNIT_EXPECT_GE(test, desc->depth, 1); in irq_free_disabled_test()
110 KUNIT_EXPECT_EQ(test, desc->depth, 0); in irq_free_disabled_test()
143 KUNIT_EXPECT_EQ(test, desc->depth, 0); in irq_shutdown_depth_test()
146 KUNIT_EXPECT_EQ(test, desc->depth, 1); in irq_shutdown_depth_test()
159 KUNIT_EXPECT_EQ(test, desc->depth, 1); in irq_shutdown_depth_test()
[all …]
|
| /linux/drivers/net/wireless/broadcom/brcm80211/brcmfmac/ |
| H A D | commonring.c | 31 void brcmf_commonring_config(struct brcmf_commonring *commonring, u16 depth, in brcmf_commonring_config() argument
34 commonring->depth = depth; in brcmf_commonring_config()
75 available = commonring->depth - commonring->w_ptr + in brcmf_commonring_write_available()
83 if (available > commonring->depth / 8) { in brcmf_commonring_write_available()
116 available = commonring->depth - commonring->w_ptr + in brcmf_commonring_reserve_for_write()
125 if (commonring->w_ptr == commonring->depth) in brcmf_commonring_reserve_for_write()
152 available = commonring->depth - commonring->w_ptr + in brcmf_commonring_reserve_for_write_multiple()
161 if (*alloced + commonring->w_ptr > commonring->depth) in brcmf_commonring_reserve_for_write_multiple()
162 *alloced = commonring->depth - commonring->w_ptr; in brcmf_commonring_reserve_for_write_multiple()
164 if (commonring->w_ptr == commonring->depth) in brcmf_commonring_reserve_for_write_multiple()
[all …]
|
| /linux/arch/s390/kernel/ |
| H A D | trace.c | 20 unsigned int *depth; in trace_s390_diagnose_norecursion() local
26 depth = this_cpu_ptr(&diagnose_trace_depth); in trace_s390_diagnose_norecursion()
27 if (*depth == 0) { in trace_s390_diagnose_norecursion()
28 (*depth)++; in trace_s390_diagnose_norecursion()
30 (*depth)--; in trace_s390_diagnose_norecursion()
|
| /linux/kernel/bpf/ |
| H A D | liveness.c | 27 u32 depth; /* call depth (0 = entry subprog) */ member
54 static u32 instance_hash(u32 callsite, u32 depth) in instance_hash() argument
56 u32 key[2] = { depth, callsite }; in instance_hash()
62 u32 callsite, u32 depth) in find_instance() argument
66 u32 key = instance_hash(callsite, depth); in find_instance()
69 if (f->depth == depth && f->callsite == callsite) in find_instance()
78 u32 depth = caller ? caller->depth + 1 : 0; in call_instance() local
80 u32 lookup_key = depth > 0 ? callsite : subprog_start; in call_instance()
84 f = find_instance(env, lookup_key, depth); in call_instance()
92 f->depth = depth; in call_instance()
[all …]
|
| /linux/sound/isa/gus/ |
| H A D | gus_volume.c | 124 long depth;
140 depth = (((int) (*(vi2 + 1) - *vi1) * (pcents - *vi1) / (*vi2 - *vi1)) + v1) * fc_register >> 14;
141 if (depth)
142 depth++;
143 if (depth > 255)
144 depth = 255;
145 return cents < 0 ? -(short) depth : (short) depth;
|
| /linux/drivers/video/fbdev/core/ |
| H A D | fb_logo.c | 99 int depth) in fb_set_logo() argument
122 switch (depth) { in fb_set_logo()
175 int depth; member
291 image.depth = 8; in fb_show_logo_line()
312 if (fb_logo.depth <= 4) { in fb_show_logo_line()
322 fb_set_logo(info, logo, logo_new, fb_logo.depth); in fb_show_logo_line()
420 int depth = fb_get_color_depth(&info->var, &info->fix); in fb_prepare_logo() local
431 depth = info->var.blue.length; in fb_prepare_logo()
432 if (info->var.red.length < depth) in fb_prepare_logo()
433 depth = info->var.red.length; in fb_prepare_logo()
[all …]
|
| /linux/drivers/net/ethernet/netronome/nfp/nfpcore/ |
| H A D | nfp_mutex.c | 17 u16 depth; member
151 mutex->depth = 0; in nfp_cpp_mutex_alloc()
199 mutex->depth, in nfp_cpp_mutex_lock()
228 if (mutex->depth > 1) { in nfp_cpp_mutex_unlock()
229 mutex->depth--; in nfp_cpp_mutex_unlock()
252 mutex->depth = 0; in nfp_cpp_mutex_unlock()
271 if (mutex->depth > 0) { in nfp_cpp_mutex_trylock()
272 if (mutex->depth == NFP_MUTEX_DEPTH_MAX) in nfp_cpp_mutex_trylock()
274 mutex->depth++; in nfp_cpp_mutex_trylock()
323 mutex->depth = 1; in nfp_cpp_mutex_trylock()
|
| /linux/kernel/locking/ |
| H A D | lockdep.c | 788 int i, depth = READ_ONCE(p->lockdep_depth); in lockdep_print_held_locks() local
790 if (!depth) in lockdep_print_held_locks()
793 printk("%d lock%s held by %s/%d:\n", depth, in lockdep_print_held_locks()
794 str_plural(depth), p->comm, task_pid_nr(p)); in lockdep_print_held_locks()
801 for (i = 0; i < depth; i++) { in lockdep_print_held_locks()
1054 for (i = chain->base; i < chain->base + chain->depth; i++) in check_lock_chain_key()
1551 int depth = 0; in get_lock_depth() local
1556 depth++; in get_lock_depth()
1558 return depth; in get_lock_depth()
1876 print_circular_bug_entry(struct lock_list *target, int depth) in print_circular_bug_entry() argument
[all …]
|
| /linux/drivers/infiniband/hw/efa/ |
| H A D | efa_com.c | 132 u16 size = aq->depth * sizeof(*sq->entries); in efa_com_admin_init_sq()
156 EFA_SET(&aq_caps, EFA_REGS_AQ_CAPS_AQ_DEPTH, aq->depth); in efa_com_admin_init_sq()
169 u16 size = aq->depth * sizeof(*cq->entries); in efa_com_admin_init_cq()
190 EFA_SET(&acq_caps, EFA_REGS_ACQ_CAPS_ACQ_DEPTH, aq->depth); in efa_com_admin_init_cq()
221 aenq->depth = EFA_ASYNC_QUEUE_DEPTH; in efa_com_admin_init_aenq()
231 EFA_SET(&aenq_caps, EFA_REGS_AENQ_CAPS_AENQ_DEPTH, aenq->depth); in efa_com_admin_init_aenq()
308 u16 ctx_id = cmd_id & (aq->depth - 1); in efa_com_get_comp_ctx_by_cmd_id()
326 queue_size_mask = aq->depth - 1; in __efa_com_submit_admin_cmd()
332 cmd_id |= aq->sq.pc << ilog2(aq->depth); in __efa_com_submit_admin_cmd()
363 size_t pool_size = aq->depth * sizeof(*aq->comp_ctx_pool); in efa_com_init_comp_ctxt()
[all …]
|
| /linux/arch/xtensa/kernel/ |
| H A D | stacktrace.c | 28 void xtensa_backtrace_user(struct pt_regs *regs, unsigned int depth, in xtensa_backtrace_user() argument
40 if (!depth--) in xtensa_backtrace_user()
71 for (index = WSBITS - 1; (index > 0) && depth; depth--, index--) in xtensa_backtrace_user()
92 if (!depth) in xtensa_backtrace_user()
97 while (a0 != 0 && depth--) { in xtensa_backtrace_user()
117 void xtensa_backtrace_kernel(struct pt_regs *regs, unsigned int depth, in xtensa_backtrace_kernel() argument
137 while (a1 > sp_start && a1 < sp_end && depth--) { in xtensa_backtrace_kernel()
151 xtensa_backtrace_user(regs, depth, ufn, data); in xtensa_backtrace_kernel()
|
| /linux/include/trace/events/ |
| H A D | kyber.h | 50 TP_PROTO(dev_t dev, const char *domain, unsigned int depth),
52 TP_ARGS(dev, domain, depth),
57 __field( unsigned int, depth )
63 __entry->depth = depth;
68 __entry->depth)
|
| /linux/kernel/trace/ |
| H A D | trace_functions_graph.c | 27 int depth; member
315 .depth = 0, in __trace_graph_function()
319 .depth = 0, in __trace_graph_function()
978 cpu_data->depth = call->depth - 1; in print_graph_entry_leaf()
981 if (call->depth < FTRACE_RETFUNC_DEPTH && in print_graph_entry_leaf()
982 !WARN_ON_ONCE(call->depth < 0)) in print_graph_entry_leaf()
983 cpu_data->enter_funcs[call->depth] = 0; in print_graph_entry_leaf()
990 for (i = 0; i < call->depth * TRACE_GRAPH_INDENT; i++) in print_graph_entry_leaf()
1036 cpu_data->depth = call->depth; in print_graph_entry_nested()
1039 if (call->depth < FTRACE_RETFUNC_DEPTH && in print_graph_entry_nested()
[all …]
|
| /linux/fs/configfs/ |
| H A D | symlink.c | 25 int depth = 0; in item_depth() local
26 do { depth++; } while ((p = p->ci_parent) && !configfs_is_root(p)); in item_depth()
27 return depth; in item_depth()
59 int depth, size; in configfs_get_target_path() local
62 depth = item_depth(item); in configfs_get_target_path()
63 size = item_path_length(target) + depth * 3 - 1; in configfs_get_target_path()
67 pr_debug("%s: depth = %d, size = %d\n", __func__, depth, size); in configfs_get_target_path()
69 for (s = path; depth--; s += 3) in configfs_get_target_path()
|
| /linux/drivers/gpu/drm/vmwgfx/ |
| H A D | vmw_surface_cache.h | 69 .depth = max_t(u32, base_level.depth >> mip_level, 1) in vmw_surface_get_mip_size()
84 block_size->depth = __KERNEL_DIV_ROUND_UP(pixel_size->depth, in vmw_surface_get_size_in_blocks()
85 desc->blockSize.depth); in vmw_surface_get_size_in_blocks()
132 total_size = clamped_umul32(total_size, image_blocks.depth); in vmw_surface_get_image_buffer_size()
141 total_size = clamped_umul32(slice_size, image_blocks.depth); in vmw_surface_get_image_buffer_size()
204 const u32 bd = desc->blockSize.depth; in vmw_surface_get_pixel_offset()
462 loc->z *= desc->blockSize.depth; in vmw_surface_get_loc()
497 loc->z += desc->blockSize.depth; in vmw_surface_inc_loc()
498 if (loc->z > size->depth) in vmw_surface_inc_loc()
499 loc->z = size->depth; in vmw_surface_inc_loc()
[all …]
|
| /linux/arch/sh/kernel/ |
| H A D | return_address.c | 16 void *return_address(unsigned int depth) in return_address() argument
22 for (i = 0, frame = NULL, ra = 0; i <= depth; i++) { in return_address()
41 WARN_ON(i != depth + 1); in return_address()
51 void *return_address(unsigned int depth) in return_address() argument
|
| /linux/arch/riscv/kernel/ |
| H A D | kernel_mode_vector.c | 157 int depth; in riscv_v_context_nesting_start() local
162 depth = riscv_v_ctx_get_depth(); in riscv_v_context_nesting_start()
163 if (depth == 0 && __riscv_v_vstate_check(regs->status, DIRTY)) in riscv_v_context_nesting_start()
172 u32 depth; in riscv_v_context_nesting_end() local
180 depth = riscv_v_ctx_get_depth(); in riscv_v_context_nesting_end()
181 if (depth == 0) { in riscv_v_context_nesting_end()
|
| /linux/drivers/video/fbdev/i810/ |
| H A D | i810_accel.c | 304 par->depth == 4) { in i810fb_fillrect()
309 if (par->depth == 1) in i810fb_fillrect()
316 dx = rect->dx * par->depth; in i810fb_fillrect()
317 width = rect->width * par->depth; in i810fb_fillrect()
332 par->depth == 4) { in i810fb_copyarea()
337 dx = region->dx * par->depth; in i810fb_copyarea()
338 sx = region->sx * par->depth; in i810fb_copyarea()
339 width = region->width * par->depth; in i810fb_copyarea()
373 par->depth == 4 || image->depth != 1) { in i810fb_imageblit()
391 (image->dx * par->depth); in i810fb_imageblit()
[all …]
|
| /linux/drivers/infiniband/hw/bng_re/ |
| H A D | bng_fw.h | 36 #define BNG_FW_CMDQE_BYTES(depth) ((depth) * BNG_FW_CMDQE_UNITS) argument
47 static inline u32 bng_fw_cmdqe_npages(u32 depth) in bng_fw_cmdqe_npages() argument
51 npages = BNG_FW_CMDQE_BYTES(depth) / PAGE_SIZE; in bng_fw_cmdqe_npages()
52 if (BNG_FW_CMDQE_BYTES(depth) % PAGE_SIZE) in bng_fw_cmdqe_npages()
57 static inline u32 bng_fw_cmdqe_page_size(u32 depth) in bng_fw_cmdqe_page_size() argument
59 return (bng_fw_cmdqe_npages(depth) * PAGE_SIZE); in bng_fw_cmdqe_page_size()
|
| /linux/security/integrity/ima/ |
| H A D | ima_iint.c | 49 int depth = inode->i_sb->s_stack_depth; in ima_iint_lockdep_annotate() local
51 if (WARN_ON_ONCE(depth < 0 || depth >= IMA_MAX_NESTING)) in ima_iint_lockdep_annotate()
52 depth = 0; in ima_iint_lockdep_annotate()
54 lockdep_set_class(&iint->mutex, &ima_iint_mutex_key[depth]); in ima_iint_lockdep_annotate()
|