/linux-master/arch/riscv/include/asm/ |
H A D | switch_to.h | 50 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 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/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/riscv/mm/ |
H A D | context.c | 208 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 D | prng.c | 102 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 D | cmpxchg.h | 93 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 D | debug.h | 46 struct debug_info *prev; member in struct:debug_info 432 .prev = NULL, \
|
H A D | mmu_context.h | 73 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 D | stacktrace.h | 179 unsigned long prev; \ 190 : [_prev] "=&d" (prev), CALL_FMT_##nr \
|
H A D | uaccess.h | 404 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 D | debug.c | 614 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 D | entry.S | 153 * 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 D | entry.h | 22 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 D | perf_cpum_cf.c | 869 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 D | perf_cpum_sf.c | 1277 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 D | perf_pai_crypto.c | 314 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 D | perf_pai_ext.c | 318 u64 prev, new, delta; local 320 prev = local64_read(&event->hw.prev_count); 323 delta = new - prev;
|
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);
|
H A D | vtime.c | 185 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 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/sh/include/asm/ |
H A D | futex.h | 32 u32 oldval, newval, prev; local 63 ret = futex_atomic_cmpxchg_inatomic(&prev, uaddr, oldval, newval); 64 } while (!ret && prev != oldval);
|
H A D | mmu_context.h | 109 static inline void switch_mm(struct mm_struct *prev, argument 115 if (likely(prev != next)) {
|
/linux-master/arch/sh/kernel/ |
H A D | dwarf.c | 568 * @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 D | process_32.c | 145 __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 D | mmu_context_64.h | 141 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);
|