Searched refs:prev (Results 126 - 150 of 1034) sorted by relevance

1234567891011>>

/linux-master/kernel/
H A Dscs.c133 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 Dhkdf.c124 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 Dcacheinfo.c79 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 Dsdrc2xxx.c80 u32 prev = curr_perf_level; local
84 return prev;
91 return prev;
108 return prev;
H A Dpm.h41 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 Dtlb.c137 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 Dlru_cache.c73 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 Dmkregtable.c37 * 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 Datomic32.c165 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 Dvideocodec.c113 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 Dspinlock.c40 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 Dmmu_context.h55 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 Dcputime.h45 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 Dprocess.c53 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 Debitmap.c51 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 Ddnotify.c96 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 Dswitch_to_32.h58 #define switch_to(prev, next, last) do { \
59 SWITCH_ENTER(prev); \
/linux-master/arch/nios2/mm/
H A Dmmu_context.c80 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 Ddma-fence-chain.h20 * @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 Dsparx5_sdlb.c138 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 Dexmutex.c46 (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 Dmmap.h30 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 Dvector.h240 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 Dsparsebit.c335 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 Dutil_mem.c88 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

Completed in 415 milliseconds

1234567891011>>