Searched refs:prev (Results 151 - 175 of 1036) sorted by path

1234567891011>>

/linux-master/arch/riscv/include/asm/
H A Dswitch_to.h50 static inline void __switch_to_fpu(struct task_struct *prev, argument
55 regs = task_pt_regs(prev);
56 fstate_save(prev, regs);
75 #define switch_to(prev, next, last) \
77 struct task_struct *__prev = (prev); \
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/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/riscv/mm/
H A Dcontext.c208 static inline void set_mm(struct mm_struct *prev, argument
223 cpumask_clear_cpu(cpu, mm_cpumask(prev));
279 static inline void set_mm(struct mm_struct *prev, argument
318 void switch_mm(struct mm_struct *prev, struct mm_struct *next, argument
323 if (unlikely(prev == next))
326 membarrier_arch_switch_mm(prev, next, task);
335 set_mm(prev, next, cpu);
/linux-master/arch/s390/crypto/
H A Dprng.c102 u8 *prev; member in struct:prng_data_s
428 prng_data->prev = prng_data->buf + prng_chunk_size;
431 prng_data->prev, prng_chunk_size, NULL, 0);
493 if (!memcmp(prng_data->prev, buf, nbytes)) {
497 memcpy(prng_data->prev, buf, nbytes);
/linux-master/arch/s390/include/asm/
H A Dcmpxchg.h93 unsigned int prev, shift, mask; local
101 " l %[prev],%[address]\n"
102 " nr %[prev],%[mask]\n"
104 " or %[new],%[prev]\n"
105 " or %[prev],%[tmp]\n"
106 "0: lr %[tmp],%[prev]\n"
107 " cs %[prev],%[new],%[address]\n"
109 " xr %[tmp],%[prev]\n"
114 : [prev] "=&d" (prev),
123 unsigned int prev, shift, mask; local
153 unsigned int prev = old; local
164 unsigned long prev = old; local
[all...]
H A Ddebug.h46 struct debug_info *prev; member in struct:debug_info
432 .prev = NULL, \
H A Dmmu_context.h73 static inline void switch_mm_irqs_off(struct mm_struct *prev, struct mm_struct *next, argument
85 if (prev != next)
86 cpumask_clear_cpu(cpu, &prev->context.cpu_attach_mask);
90 static inline void switch_mm(struct mm_struct *prev, struct mm_struct *next, argument
96 switch_mm_irqs_off(prev, next, tsk);
118 static inline void activate_mm(struct mm_struct *prev, argument
121 switch_mm(prev, next, current);
H A Dstacktrace.h179 unsigned long prev; \
190 : [_prev] "=&d" (prev), CALL_FMT_##nr \
H A Duaccess.h404 unsigned int prev, shift, mask, _old, _new; local
416 "0: l %[prev],%[address]\n"
417 "1: nr %[prev],%[mask]\n"
419 " or %[new],%[prev]\n"
420 " or %[prev],%[tmp]\n"
421 "2: lr %[tmp],%[prev]\n"
422 "3: cs %[prev],%[new],%[address]\n"
424 " xr %[tmp],%[prev]\n"
431 EX_TABLE_UA_LOAD_REG(0b, 5b, %[rc], %[prev])
432 EX_TABLE_UA_LOAD_REG(1b, 5b, %[rc], %[prev])
452 unsigned int prev, shift, mask, _old, _new; local
500 unsigned int prev = old; local
521 unsigned long prev = old; local
542 __uint128_t prev = old; local
[all...]
/linux-master/arch/s390/kernel/
H A Ddebug.c614 id->prev = NULL;
618 id->prev = debug_area_last;
764 debug_area_last = id->prev;
765 if (id->prev)
766 id->prev->next = id->next;
768 id->next->prev = id->prev;
H A Dentry.S153 * gpr2 = (task_struct *)prev
156 * gpr2 = prev
159 stmg %r6,%r15,__SF_GPRS(%r15) # store gprs of prev task
163 stg %r15,__THREAD_ksp(%r1,%r2) # store kernel stack of prev
H A Dentry.h22 struct task_struct *__switch_to_asm(struct task_struct *prev, struct task_struct *next);
23 void __ret_from_fork(struct task_struct *prev, struct pt_regs *regs);
H A Dperf_cpum_cf.c869 u64 prev, new; local
873 prev = local64_read(&event->hw.prev_count);
885 } while (local64_cmpxchg(&event->hw.prev_count, prev, new) != prev);
892 u64 prev, new, delta; local
896 prev = local64_read(&event->hw.prev_count);
900 } while (local64_cmpxchg(&event->hw.prev_count, prev, new) != prev);
902 delta = (prev <= new) ? new - prev
[all...]
H A Dperf_cpum_sf.c1277 union hws_trailer_header old, prev, new; local
1327 prev.val = READ_ONCE_ALIGNED_128(te->header.val);
1329 old.val = prev.val;
1330 new.val = prev.val;
1334 prev.val = cmpxchg128(&te->header.val, old.val, new.val);
1335 } while (prev.val != old.val);
1525 union hws_trailer_header old, prev, new; local
1529 prev.val = READ_ONCE_ALIGNED_128(te->header.val);
1531 old.val = prev.val;
1532 new.val = prev
1575 union hws_trailer_header old, prev, new; local
[all...]
H A Dperf_pai_crypto.c314 u64 prev, new, delta; local
316 prev = local64_read(&event->hw.prev_count);
319 delta = (prev <= new) ? new - prev
320 : (-1ULL - prev) + new + 1; /* overflow */
H A Dperf_pai_ext.c318 u64 prev, new, delta; local
320 prev = local64_read(&event->hw.prev_count);
323 delta = new - prev;
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);
H A Dvtime.c185 void vtime_task_switch(struct task_struct *prev) argument
187 do_account_vtime(prev);
188 prev->thread.user_timer = S390_lowcore.user_timer;
189 prev->thread.guest_timer = S390_lowcore.guest_timer;
190 prev->thread.system_timer = S390_lowcore.system_timer;
191 prev->thread.hardirq_timer = S390_lowcore.hardirq_timer;
192 prev->thread.softirq_timer = S390_lowcore.softirq_timer;
/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/sh/include/asm/
H A Dfutex.h32 u32 oldval, newval, prev; local
63 ret = futex_atomic_cmpxchg_inatomic(&prev, uaddr, oldval, newval);
64 } while (!ret && prev != oldval);
H A Dmmu_context.h109 static inline void switch_mm(struct mm_struct *prev, argument
115 if (likely(prev != next)) {
/linux-master/arch/sh/kernel/
H A Ddwarf.c568 * @prev: struct dwarf_frame of the previous stackframe on the callstack
572 * linked via the "prev" member.
575 struct dwarf_frame *prev)
598 if (!pc || !prev)
631 frame->prev = prev;
670 if (prev) {
671 reg = dwarf_frame_reg(prev, frame->cfa_register);
675 addr = prev->cfa + reg->addr;
725 if (prev
574 dwarf_unwind_stack(unsigned long pc, struct dwarf_frame *prev) argument
[all...]
H A Dprocess_32.c145 __switch_to(struct task_struct *prev, struct task_struct *next) argument
153 unlazy_fpu(prev, task_pt_regs(prev));
177 return prev;
/linux-master/arch/sparc/include/asm/
H A Dmmu_context_64.h141 static inline void arch_start_context_switch(struct task_struct *prev) argument
156 set_tsk_thread_flag(prev, TIF_MCDPER);
158 clear_tsk_thread_flag(prev, TIF_MCDPER);

Completed in 457 milliseconds

1234567891011>>