/linux-master/kernel/ |
H A D | scs.c | 133 unsigned long *p, prev, curr = highest, used = 0; local 145 prev = cmpxchg_relaxed(&highest, curr, used); 147 if (prev == curr) { 153 curr = prev;
|
/linux-master/fs/crypto/ |
H A D | hkdf.c | 124 const u8 *prev = NULL; local 142 if (prev) { 143 err = crypto_shash_update(desc, prev, HKDF_HASHLEN); 169 prev = &okm[i];
|
/linux-master/arch/riscv/kernel/ |
H A D | cacheinfo.c | 79 struct device_node *prev = NULL; local 89 prev = np; 91 of_node_put(prev); 92 prev = np;
|
/linux-master/arch/arm/mach-omap2/ |
H A D | sdrc2xxx.c | 80 u32 prev = curr_perf_level; local 84 return prev; 91 return prev; 108 return prev;
|
H A D | pm.h | 41 extern void pm_dbg_update_time(struct powerdomain *pwrdm, int prev); 43 #define pm_dbg_update_time(pwrdm, prev) do {} while (0);
|
/linux-master/arch/openrisc/mm/ |
H A D | tlb.c | 137 void switch_mm(struct mm_struct *prev, struct mm_struct *next, argument 142 if (unlikely(prev == next)) 147 cpumask_clear_cpu(cpu, mm_cpumask(prev)); 161 local_flush_tlb_mm(prev);
|
/linux-master/fs/btrfs/ |
H A D | lru_cache.c | 73 struct list_head *prev = entry->list.prev; local 81 if (list_empty(prev)) { 90 ASSERT(head == prev);
|
/linux-master/drivers/gpu/drm/radeon/ |
H A D | mkregtable.c | 37 * sometimes we already know the next/prev entries and we can 43 struct list_head *next, *prev; member in struct:list_head 50 list->prev = list; 57 * the prev/next entries already! 61 struct list_head *prev, struct list_head *next) 63 next->prev = new; 65 new->prev = prev; 66 prev->next = new; 70 struct list_head *prev, struc 60 __list_add(struct list_head *new, struct list_head *prev, struct list_head *next) argument [all...] |
/linux-master/arch/sparc/lib/ |
H A D | atomic32.c | 165 u32 prev; local 168 if ((prev = *ptr) == old) 172 return (unsigned long)prev; 179 u64 prev; local 182 if ((prev = *ptr) == old) 186 return prev; 193 u32 prev; local 196 prev = *ptr; 200 return (unsigned long)prev;
|
/linux-master/drivers/media/pci/zoran/ |
H A D | videocodec.c | 113 struct attached_list *a, *prev; local 133 prev = NULL; 145 if (!prev) { 149 prev->next = a->next; 157 prev = a; 204 struct codec_list *prev = NULL, *h = codeclist_top; local 232 if (!prev) { 237 prev->next = h->next; 244 prev = h;
|
/linux-master/arch/s390/lib/ |
H A D | spinlock.c | 40 struct spin_wait *next, *prev; member in struct:spin_wait 110 if (node == NULL || node->prev == NULL) 112 while (node->prev) 113 node = node->prev; 126 node->prev = node->next = NULL; 156 node->prev = arch_spin_decode_tail(tail_id); 157 WRITE_ONCE(node->prev->next, node); 165 /* Spin on the CPU local node->prev pointer */ 168 while (READ_ONCE(node->prev) != NULL) { 204 next->prev [all...] |
/linux-master/arch/powerpc/include/asm/ |
H A D | mmu_context.h | 55 extern void radix__switch_mmu_context(struct mm_struct *prev, 57 static inline void switch_mmu_context(struct mm_struct *prev, argument 62 return radix__switch_mmu_context(prev, next); 100 extern void switch_mmu_context(struct mm_struct *prev, struct mm_struct *next, 226 extern void switch_mm_irqs_off(struct mm_struct *prev, struct mm_struct *next, 229 static inline void switch_mm(struct mm_struct *prev, struct mm_struct *next, 235 switch_mm_irqs_off(prev, next, tsk); 245 static inline void activate_mm(struct mm_struct *prev, struct mm_struct *next) 247 switch_mm_irqs_off(prev, next, current);
|
H A D | cputime.h | 45 static inline void arch_vtime_task_switch(struct task_struct *prev) argument 48 struct cpu_accounting_data *acct0 = get_accounting(prev);
|
/linux-master/arch/s390/kernel/ |
H A D | process.c | 53 void __ret_from_fork(struct task_struct *prev, struct pt_regs *regs) argument 57 schedule_tail(prev); 197 struct task_struct *__switch_to(struct task_struct *prev, struct task_struct *next) argument 200 save_kernel_fpu_regs(&prev->thread); 201 save_access_regs(&prev->thread.acrs[0]); 202 save_ri_cb(prev->thread.ri_cb); 203 save_gs_cb(prev->thread.gs_cb); 207 restore_ri_cb(next->thread.ri_cb, prev->thread.ri_cb); 209 return __switch_to_asm(prev, next);
|
/linux-master/security/selinux/ss/ |
H A D | ebitmap.c | 51 struct ebitmap_node *new, *prev; local 56 prev = NULL; 66 if (prev) 67 prev->next = new; 70 prev = new; 278 struct ebitmap_node *n, *prev, *new; local 280 prev = NULL; 301 if (prev) 302 e->highbit = prev->startbit + 307 if (prev) [all...] |
/linux-master/fs/notify/dnotify/ |
H A D | dnotify.c | 96 struct dnotify_struct **prev; local 107 prev = &dn_mark->dn; 108 while ((dn = *prev) != NULL) { 110 prev = &dn->dn_next; 116 prev = &dn->dn_next; 118 *prev = dn->dn_next; 157 struct dnotify_struct **prev; local 173 prev = &dn_mark->dn; 174 while ((dn = *prev) != NULL) { 176 *prev [all...] |
/linux-master/arch/sparc/include/asm/ |
H A D | switch_to_32.h | 58 #define switch_to(prev, next, last) do { \ 59 SWITCH_ENTER(prev); \
|
/linux-master/arch/nios2/mm/ |
H A D | mmu_context.c | 80 void switch_mm(struct mm_struct *prev, struct mm_struct *next, argument 106 void activate_mm(struct mm_struct *prev, struct mm_struct *next) argument
|
/linux-master/include/linux/ |
H A D | dma-fence-chain.h | 20 * @prev: previous fence of the chain 27 struct dma_fence __rcu *prev; member in struct:dma_fence_chain 125 struct dma_fence *prev,
|
/linux-master/drivers/net/ethernet/microchip/sparx5/ |
H A D | sparx5_sdlb.c | 138 u32 idx, u32 *prev, u32 *next, 144 *prev = *first; 157 *prev = itr; 275 u32 first, next, prev; local 278 if (sparx5_sdlb_group_get_adjacent(sparx5, group, idx, &prev, &next, 288 /* idx is removed, prev is now last */ 289 idx = prev; 290 next = prev; 297 idx = prev; 137 sparx5_sdlb_group_get_adjacent(struct sparx5 *sparx5, u32 group, u32 idx, u32 *prev, u32 *next, u32 *first) argument
|
/linux-master/drivers/acpi/acpica/ |
H A D | exmutex.c | 46 (obj_desc->mutex.next)->mutex.prev = obj_desc->mutex.prev; 49 if (obj_desc->mutex.prev) { 50 (obj_desc->mutex.prev)->mutex.next = obj_desc->mutex.next; 58 (obj_desc->mutex.prev)->mutex.original_sync_level = 88 obj_desc->mutex.prev = NULL; 94 list_head->mutex.prev = obj_desc; 498 obj_desc->mutex.prev = NULL;
|
/linux-master/tools/lib/perf/include/internal/ |
H A D | mmap.h | 30 u64 prev; member in struct:perf_mmap 48 void perf_mmap__init(struct perf_mmap *map, struct perf_mmap *prev,
|
/linux-master/arch/riscv/include/asm/ |
H A D | vector.h | 240 static inline void __switch_to_vector(struct task_struct *prev, argument 245 if (riscv_preempt_v_started(prev)) { 246 if (riscv_preempt_v_dirty(prev)) { 247 __riscv_v_vstate_save(&prev->thread.kernel_vstate, 248 prev->thread.kernel_vstate.datap); 249 riscv_preempt_v_clear_dirty(prev); 252 regs = task_pt_regs(prev); 253 riscv_v_vstate_save(&prev->thread.vstate, regs);
|
/linux-master/tools/testing/selftests/kvm/lib/ |
H A D | sparsebit.c | 335 struct node *nodep, *parentp, *prev; local 381 prev = node_prev(s, nodep); 382 while (prev && prev->idx + MASK_BITS + prev->num_after - 1 >= nodep->idx) { 383 unsigned int n1 = (prev->idx + MASK_BITS + prev->num_after - 1) 385 assert(prev->num_after > 0); 389 prev->num_after--; 605 struct node *prev, *nex local 1154 sparsebit_next_set(const struct sparsebit *s, sparsebit_idx_t prev) argument 1247 sparsebit_next_clear(const struct sparsebit *s, sparsebit_idx_t prev) argument 1687 struct node *nodep, *prev = NULL; local [all...] |
/linux-master/sound/synth/ |
H A D | util_mem.c | 88 return __snd_util_memblk_new(hdr, units, p->prev); 94 * the block is linked next to prev 98 struct list_head *prev) 107 if (prev == &hdr->block) 110 struct snd_util_memblk *p = get_memblk(prev); 114 list_add(&blk->list, prev); 97 __snd_util_memblk_new(struct snd_util_memhdr *hdr, unsigned int units, struct list_head *prev) argument
|