arch/alpha/include/asm/processor.h

37

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->pc)

arch/alpha/kernel/process.c

241

struct pt_regs *childregs = task_pt_regs(p);

arch/alpha/kernel/process.c

334

dump_elf_thread(dest, task_pt_regs(task), task_thread_info(task));

arch/arc/include/asm/processor.h

49

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->ret)

arch/arc/include/asm/processor.h

50

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->sp)

arch/arc/kernel/kgdb.c

73

to_gdb_regs(gdb_regs, task_pt_regs(task),

arch/arc/kernel/process.c

179

c_regs = task_pt_regs(p);

arch/arc/kernel/ptrace.c

106

const struct pt_regs *ptregs = task_pt_regs(target);

arch/arc/kernel/ptrace.c

166

const struct pt_regs *ptregs = task_pt_regs(target);

arch/arc/kernel/ptrace.c

245

const struct pt_regs *regs = task_pt_regs(target);

arch/arc/kernel/ptrace.c

264

const struct pt_regs *regs = task_pt_regs(target);

arch/arm/include/asm/processor.h

90

#define KSTK_EIP(tsk) task_pt_regs(tsk)->ARM_pc

arch/arm/include/asm/processor.h

91

#define KSTK_ESP(tsk) task_pt_regs(tsk)->ARM_sp

arch/arm/kernel/perf_regs.c

37

regs_user->regs = task_pt_regs(current);

arch/arm/kernel/process.c

241

struct pt_regs *childregs = task_pt_regs(p);

arch/arm/kernel/ptrace.c

163

return task_pt_regs(task)->uregs[offset];

arch/arm/kernel/ptrace.c

175

struct pt_regs newregs, *regs = task_pt_regs(task);

arch/arm/kernel/ptrace.c

548

return membuf_write(&to, task_pt_regs(target), sizeof(struct pt_regs));

arch/arm/kernel/ptrace.c

557

struct pt_regs newregs = *task_pt_regs(target);

arch/arm/kernel/ptrace.c

568

*task_pt_regs(target) = newregs;

arch/arm64/include/asm/compat.h

86

#define compat_user_stack_pointer() (user_stack_pointer(task_pt_regs(current)))

arch/arm64/include/asm/processor.h

386

#define KSTK_EIP(tsk) ((unsigned long)task_pt_regs(tsk)->pc)

arch/arm64/include/asm/processor.h

387

#define KSTK_ESP(tsk) user_stack_pointer(task_pt_regs(tsk))

arch/arm64/kernel/debug-monitors.c

327

set_regs_spsr_ss(task_pt_regs(task));

arch/arm64/kernel/debug-monitors.c

334

clear_regs_spsr_ss(task_pt_regs(task));

arch/arm64/kernel/debug-monitors.c

387

set_regs_spsr_ss(task_pt_regs(task));

arch/arm64/kernel/perf_regs.c

104

regs_user->regs = task_pt_regs(current);

arch/arm64/kernel/process.c

416

struct pt_regs *childregs = task_pt_regs(p);

arch/arm64/kernel/proton-pack.c

658

struct pt_regs *regs = task_pt_regs(tsk);

arch/arm64/kernel/ptrace.c

1805

struct pt_regs *regs = task_pt_regs(task);

arch/arm64/kernel/ptrace.c

1848

newregs = *task_pt_regs(target);

arch/arm64/kernel/ptrace.c

1885

*task_pt_regs(target) = newregs;

arch/arm64/kernel/ptrace.c

2082

struct pt_regs newregs = *task_pt_regs(tsk);

arch/arm64/kernel/ptrace.c

2108

*task_pt_regs(tsk) = newregs;

arch/arm64/kernel/ptrace.c

2274

task_pt_regs(child)->syscallno = data;

arch/arm64/kernel/ptrace.c

559

struct user_pt_regs *uregs = &task_pt_regs(target)->user_regs;

arch/arm64/kernel/ptrace.c

568

struct user_pt_regs newregs = task_pt_regs(target)->user_regs;

arch/arm64/kernel/ptrace.c

577

task_pt_regs(target)->user_regs = newregs;

arch/arm64/kernel/ptrace.c

740

return membuf_store(&to, task_pt_regs(target)->syscallno);

arch/arm64/kernel/ptrace.c

748

int syscallno = task_pt_regs(target)->syscallno;

arch/arm64/kernel/ptrace.c

755

task_pt_regs(target)->syscallno = syscallno;

arch/arm64/kernel/stacktrace.c

204

if (meta == &task_pt_regs(tsk)->stackframe)

arch/arm64/kernel/traps.c

243

struct pt_regs *regs = task_pt_regs(tsk);

arch/csky/include/asm/processor.h

77

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->pc)

arch/csky/include/asm/processor.h

78

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->usp)

arch/csky/kernel/perf_regs.c

37

regs_user->regs = task_pt_regs(current);

arch/csky/kernel/process.c

39

struct pt_regs *childregs = task_pt_regs(p);

arch/csky/kernel/process.c

81

struct pt_regs *regs = task_pt_regs(tsk);

arch/csky/kernel/ptrace.c

102

regs.sr = (regs.sr & BIT(0)) | (task_pt_regs(target)->sr & ~BIT(0));

arch/csky/kernel/ptrace.c

104

regs.dcsr = task_pt_regs(target)->dcsr;

arch/csky/kernel/ptrace.c

108

*task_pt_regs(target) = regs;

arch/csky/kernel/ptrace.c

41

regs = task_pt_regs(tsk);

arch/csky/kernel/ptrace.c

52

regs = task_pt_regs(tsk);

arch/csky/kernel/ptrace.c

81

struct pt_regs *regs = task_pt_regs(target);

arch/hexagon/include/asm/processor.h

60

#define KSTK_EIP(tsk) (pt_elr(task_pt_regs(tsk)))

arch/hexagon/include/asm/processor.h

61

#define KSTK_ESP(tsk) (pt_psp(task_pt_regs(tsk)))

arch/hexagon/kernel/kgdb.c

119

thread_regs = task_pt_regs(task);

arch/hexagon/kernel/ptrace.c

25

pt_set_singlestep(task_pt_regs(child));

arch/hexagon/kernel/ptrace.c

31

pt_clr_singlestep(task_pt_regs(child));

arch/hexagon/kernel/ptrace.c

40

struct pt_regs *regs = task_pt_regs(target);

arch/hexagon/kernel/ptrace.c

79

struct pt_regs *regs = task_pt_regs(target);

arch/loongarch/include/asm/processor.h

204

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->csr_era)

arch/loongarch/include/asm/processor.h

205

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->regs[3])

arch/loongarch/include/asm/processor.h

206

#define KSTK_EUEN(tsk) (task_pt_regs(tsk)->csr_euen)

arch/loongarch/include/asm/processor.h

207

#define KSTK_ECFG(tsk) (task_pt_regs(tsk)->csr_ecfg)

arch/loongarch/kernel/hw_breakpoint.c

202

regs = task_pt_regs(bp->hw.target);

arch/loongarch/kernel/hw_breakpoint.c

548

struct pt_regs *regs = task_pt_regs(next);

arch/loongarch/kernel/machine_kexec.c

161

regs = task_pt_regs(current);

arch/loongarch/kernel/perf_regs.c

51

regs_user->regs = task_pt_regs(current);

arch/loongarch/kernel/ptrace.c

1086

set_single_step(task, task_pt_regs(task)->csr_era);

arch/loongarch/kernel/ptrace.c

1087

task->thread.single_step = task_pt_regs(task)->csr_era;

arch/loongarch/kernel/ptrace.c

80

struct pt_regs *regs = task_pt_regs(target);

arch/loongarch/kernel/ptrace.c

965

tmp = task_pt_regs(target)->regs[addr];

arch/loongarch/kernel/ptrace.c

968

tmp = task_pt_regs(target)->orig_a0;

arch/loongarch/kernel/ptrace.c

971

tmp = task_pt_regs(target)->csr_era;

arch/loongarch/kernel/ptrace.c

974

tmp = task_pt_regs(target)->csr_badvaddr;

arch/loongarch/kernel/ptrace.c

988

task_pt_regs(target)->regs[addr] = data;

arch/loongarch/kernel/ptrace.c

99

struct pt_regs *regs = task_pt_regs(target);

arch/loongarch/kernel/ptrace.c

991

task_pt_regs(target)->orig_a0 = data;

arch/loongarch/kernel/ptrace.c

994

task_pt_regs(target)->csr_era = data;

arch/loongarch/kernel/ptrace.c

997

task_pt_regs(target)->csr_badvaddr = data;

arch/m68k/kernel/ptrace.c

282

ret = ptrace_report_syscall_entry(task_pt_regs(current));

arch/m68k/kernel/ptrace.c

293

ptrace_report_syscall_exit(task_pt_regs(current), 0);

arch/m68k/kernel/ptrace.c

306

struct pt_regs *ptregs = task_pt_regs(target);

arch/microblaze/include/asm/processor.h

76

((void *)task_pt_regs(tsk))

arch/microblaze/kernel/process.c

60

struct pt_regs *childregs = task_pt_regs(p);

arch/microblaze/kernel/ptrace.c

72

regs = task_pt_regs(t);

arch/microblaze/kernel/unwind.c

236

if (unlikely(pc == task_pt_regs(task)->pc)) {

arch/microblaze/kernel/unwind.c

278

const struct pt_regs *regs = task_pt_regs(task);

arch/mips/include/asm/processor.h

366

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->cp0_epc)

arch/mips/include/asm/processor.h

367

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->regs[29])

arch/mips/include/asm/processor.h

368

#define KSTK_STATUS(tsk) (task_pt_regs(tsk)->cp0_status)

arch/mips/include/asm/switch_to.h

94

pc = (void __user *)task_pt_regs(next)->cp0_epc; \

arch/mips/kernel/crash.c

34

regs = task_pt_regs(current);

arch/mips/kernel/perf_regs.c

66

regs_user->regs = task_pt_regs(current);

arch/mips/kernel/ptrace.c

109

regs = task_pt_regs(child);

arch/mips/kernel/ptrace.c

1104

regs = task_pt_regs(child);

arch/mips/kernel/ptrace.c

1203

regs = task_pt_regs(child);

arch/mips/kernel/ptrace.c

221

struct pt_regs *regs = task_pt_regs(target);

arch/mips/kernel/ptrace.c

233

struct pt_regs *regs = task_pt_regs(target);

arch/mips/kernel/ptrace.c

286

struct pt_regs *regs = task_pt_regs(target);

arch/mips/kernel/ptrace.c

298

struct pt_regs *regs = task_pt_regs(target);

arch/mips/kernel/ptrace.c

82

regs = task_pt_regs(child);

arch/mips/kernel/ptrace32.c

197

regs = task_pt_regs(child);

arch/mips/kernel/ptrace32.c

86

regs = task_pt_regs(child);

arch/nios2/kernel/process.c

107

struct pt_regs *childregs = task_pt_regs(p);

arch/nios2/kernel/ptrace.c

136

ret = ptrace_report_syscall_entry(task_pt_regs(current));

arch/nios2/kernel/ptrace.c

144

ptrace_report_syscall_exit(task_pt_regs(current), 0);

arch/nios2/kernel/ptrace.c

25

const struct pt_regs *regs = task_pt_regs(target);

arch/nios2/kernel/ptrace.c

51

struct pt_regs *regs = task_pt_regs(target);

arch/openrisc/include/asm/processor.h

71

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->pc)

arch/openrisc/include/asm/processor.h

72

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->sp)

arch/openrisc/kernel/ptrace.c

52

const struct pt_regs *regs = task_pt_regs(target);

arch/openrisc/kernel/ptrace.c

69

struct pt_regs *regs = task_pt_regs(target);

arch/parisc/kernel/kgdb.c

129

struct pt_regs *regs = task_pt_regs(task);

arch/parisc/kernel/perf_regs.c

59

regs_user->regs = task_pt_regs(current);

arch/powerpc/perf/perf_regs.c

146

regs_user->regs = task_pt_regs(current);

arch/riscv/include/asm/processor.h

145

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->epc)

arch/riscv/include/asm/processor.h

146

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->sp)

arch/riscv/include/asm/switch_to.h

56

regs = task_pt_regs(prev);

arch/riscv/include/asm/switch_to.h

58

fstate_restore(next, task_pt_regs(next));

arch/riscv/include/asm/vector.h

386

regs = task_pt_regs(prev);

arch/riscv/include/asm/vector.h

398

riscv_v_vstate_set_restore(next, task_pt_regs(next));

arch/riscv/kernel/cpu_ops_sbi.c

75

bdata->stack_ptr = task_pt_regs(tidle);

arch/riscv/kernel/cpu_ops_spinwait.c

37

WRITE_ONCE(__cpu_spinwait_stack_pointer[hartid], task_pt_regs(tidle));

arch/riscv/kernel/kernel_mode_fpu.c

17

fstate_save(current, task_pt_regs(current));

arch/riscv/kernel/kernel_mode_fpu.c

25

fstate_restore(current, task_pt_regs(current));

arch/riscv/kernel/kernel_mode_vector.c

146

if (__riscv_v_vstate_check(task_pt_regs(current)->status, DIRTY)) {

arch/riscv/kernel/kernel_mode_vector.c

218

riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));

arch/riscv/kernel/kernel_mode_vector.c

222

riscv_v_vstate_set_restore(current, task_pt_regs(current));

arch/riscv/kernel/perf_regs.c

41

regs_user->regs = task_pt_regs(current);

arch/riscv/kernel/process.c

190

fstate_off(current, task_pt_regs(current));

arch/riscv/kernel/process.c

196

riscv_v_vstate_off(task_pt_regs(current));

arch/riscv/kernel/process.c

216

fstate_save(src, task_pt_regs(src));

arch/riscv/kernel/process.c

244

struct pt_regs *childregs = task_pt_regs(p);

arch/riscv/kernel/ptrace.c

105

if (!riscv_v_vstate_query(task_pt_regs(target)))

arch/riscv/kernel/ptrace.c

114

riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));

arch/riscv/kernel/ptrace.c

229

if (!riscv_v_vstate_query(task_pt_regs(target)))

arch/riscv/kernel/ptrace.c

258

if (!riscv_v_vstate_query(task_pt_regs(target)))

arch/riscv/kernel/ptrace.c

303

regs = task_pt_regs(target);

arch/riscv/kernel/ptrace.c

340

regs = task_pt_regs(target);

arch/riscv/kernel/ptrace.c

44

return membuf_write(&to, task_pt_regs(target),

arch/riscv/kernel/ptrace.c

55

regs = task_pt_regs(target);

arch/riscv/kernel/ptrace.c

565

regs_to_cregs(&cregs, task_pt_regs(target));

arch/riscv/kernel/ptrace.c

581

cregs_to_regs(&cregs, task_pt_regs(target));

arch/riscv/kernel/ptrace.c

67

fstate_save(current, task_pt_regs(current));

arch/riscv/kernel/signal.c

290

if (cal_all || riscv_v_vstate_query(task_pt_regs(current)))

arch/riscv/kernel/traps.c

49

if (regs != task_pt_regs(current))

arch/riscv/kernel/usercfi.c

219

(void *)(task_pt_regs(tsk)->epc),

arch/riscv/kernel/usercfi.c

220

(void *)(task_pt_regs(tsk)->sp),

arch/s390/include/asm/processor.h

253

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->psw.addr)

arch/s390/include/asm/processor.h

254

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->gprs[15])

arch/s390/kernel/perf_regs.c

59

regs_user->regs = task_pt_regs(current);

arch/s390/kernel/process.c

117

frame = container_of(task_pt_regs(p), struct fake_frame, childregs);

arch/s390/kernel/ptrace.c

209

tmp = *(addr_t *)((addr_t) &task_pt_regs(child)->psw + addr);

arch/s390/kernel/ptrace.c

235

tmp = (addr_t) task_pt_regs(child)->orig_gpr2;

arch/s390/kernel/ptrace.c

329

struct pt_regs *regs = task_pt_regs(child);

arch/s390/kernel/ptrace.c

350

struct pt_regs *regs = task_pt_regs(child);

arch/s390/kernel/ptrace.c

375

task_pt_regs(child)->orig_gpr2 = data;

arch/s390/kernel/ptrace.c

42

struct pt_regs *regs = task_pt_regs(task);

arch/s390/kernel/ptrace.c

623

struct pt_regs *regs = task_pt_regs(target);

arch/s390/kernel/runtime_instr.c

38

regs = task_pt_regs(task);

arch/s390/kernel/signal.c

216

struct pt_regs *regs = task_pt_regs(current);

arch/s390/kernel/signal.c

238

struct pt_regs *regs = task_pt_regs(current);

arch/s390/kernel/unwind_bc.c

45

if (task_pt_regs(state->task) == regs)

arch/s390/kernel/uprobes.c

45

struct pt_regs *regs = task_pt_regs(tsk);

arch/sh/include/asm/processor_32.h

183

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->pc)

arch/sh/include/asm/processor_32.h

184

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->regs[15])

arch/sh/kernel/cpu/fpu.c

15

unlazy_fpu(tsk, task_pt_regs(tsk));

arch/sh/kernel/kgdb.c

225

struct pt_regs *thread_regs = task_pt_regs(p);

arch/sh/kernel/process.c

26

unlazy_fpu(src, task_pt_regs(src));

arch/sh/kernel/process_32.c

112

childregs = task_pt_regs(p);

arch/sh/kernel/process_32.c

153

unlazy_fpu(prev, task_pt_regs(prev));

arch/sh/kernel/process_32.c

82

clear_fpu(tsk, task_pt_regs(tsk));

arch/sh/kernel/ptrace_32.c

138

const struct pt_regs *regs = task_pt_regs(target);

arch/sh/kernel/ptrace_32.c

148

struct pt_regs *regs = task_pt_regs(target);

arch/sh/kernel/ptrace_32.c

241

struct pt_regs *regs = task_pt_regs(target);

arch/sh/kernel/ptrace_32.c

42

stack = (unsigned char *)task_pt_regs(task);

arch/sh/kernel/ptrace_32.c

55

stack = (unsigned char *)task_pt_regs(task);

arch/sparc/include/asm/mman.h

25

regs = task_pt_regs(current);

arch/sparc/include/asm/mman.h

37

regs = task_pt_regs(current);

arch/sparc/include/asm/mmu_context_64.h

182

regs = task_pt_regs(current);

arch/sparc/include/asm/processor_64.h

182

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->tpc)

arch/sparc/include/asm/processor_64.h

183

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->u_regs[UREG_FP])

arch/sparc/kernel/ptrace_64.c

1014

unsigned long addr2 = task_pt_regs(current)->u_regs[UREG_I4];

arch/sparc/kernel/ptrace_64.c

250

const struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

272

struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

446

const struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

462

struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

536

const struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

563

struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

780

const struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

800

struct pt_regs *regs = task_pt_regs(target);

arch/sparc/kernel/ptrace_64.c

930

compat_ulong_t caddr2 = task_pt_regs(current)->u_regs[UREG_I4];

arch/x86/include/asm/compat.h

80

(!!(task_pt_regs(current)->orig_ax & __X32_SYSCALL_BIT))

arch/x86/include/asm/compat.h

86

if (task_pt_regs(current)->orig_ax & __X32_SYSCALL_BIT)

arch/x86/include/asm/elfcore-compat.h

23

(user_64bit_mode(task_pt_regs(current)) \

arch/x86/include/asm/elfcore-compat.h

27

(*(user_64bit_mode(task_pt_regs(current)) \

arch/x86/include/asm/entry-common.h

43

WARN_ON_ONCE(regs != task_pt_regs(current));

arch/x86/include/asm/processor.h

646

#define task_top_of_stack(task) ((unsigned long)(task_pt_regs(task) + 1))

arch/x86/include/asm/processor.h

680

#define KSTK_EIP(task) (task_pt_regs(task)->ip)

arch/x86/include/asm/processor.h

681

#define KSTK_ESP(task) (task_pt_regs(task)->sp)

arch/x86/kernel/dumpstack.c

80

if (regs != task_pt_regs(current))

arch/x86/kernel/fpu/regset.c

350

env->fcs = task_pt_regs(tsk)->cs;

arch/x86/kernel/perf_regs.c

106

regs_user->regs = task_pt_regs(current);

arch/x86/kernel/perf_regs.c

125

if (!user_64bit_mode(task_pt_regs(task)))

arch/x86/kernel/perf_regs.c

137

struct pt_regs *user_regs = task_pt_regs(current);

arch/x86/kernel/process.c

181

childregs = task_pt_regs(p);

arch/x86/kernel/process_64.c

723

task_pt_regs(current)->orig_ax = __NR_execve;

arch/x86/kernel/process_64.c

750

task_pt_regs(current)->orig_ax = __NR_x32_execve | __X32_SYSCALL_BIT;

arch/x86/kernel/process_64.c

768

task_pt_regs(current)->orig_ax = __NR_ia32_execve;

arch/x86/kernel/ptrace.c

1398

if (!user_64bit_mode(task_pt_regs(task)))

arch/x86/kernel/ptrace.c

190

retval = *pt_regs_access(task_pt_regs(task), offset);

arch/x86/kernel/ptrace.c

229

*pt_regs_access(task_pt_regs(task), offset) = value;

arch/x86/kernel/ptrace.c

287

return *pt_regs_access(task_pt_regs(task), offset);

arch/x86/kernel/ptrace.c

328

task_pt_regs(task)->cs = value;

arch/x86/kernel/ptrace.c

333

task_pt_regs(task)->ss = value;

arch/x86/kernel/ptrace.c

344

unsigned long retval = task_pt_regs(task)->flags;

arch/x86/kernel/ptrace.c

357

struct pt_regs *regs = task_pt_regs(task);

arch/x86/kernel/ptrace.c

403

*pt_regs_access(task_pt_regs(child), offset) = value;

arch/x86/kernel/ptrace.c

429

return *pt_regs_access(task_pt_regs(task), offset);

arch/x86/kernel/ptrace.c

875

struct pt_regs *regs = task_pt_regs(child);

arch/x86/kernel/ptrace.c

973

struct pt_regs *regs = task_pt_regs(child);

arch/x86/kernel/smpboot.c

1008

idle->thread.sp = (unsigned long)task_pt_regs(idle);

arch/x86/kernel/step.c

115

struct pt_regs *regs = task_pt_regs(child);

arch/x86/kernel/step.c

243

task_pt_regs(child)->flags &= ~X86_EFLAGS_TF;

arch/x86/kernel/unwind_frame.c

277

regs = task_pt_regs(state->task);

arch/x86/kernel/unwind_frame.c

341

state->regs->sp < (unsigned long)task_pt_regs(state->task))

arch/x86/kernel/unwind_frame.c

82

return (unsigned long *)task_pt_regs(state->task) - 2;

arch/x86/kernel/uprobes.c

352

struct pt_regs *regs = task_pt_regs(current);

arch/x86/kernel/uprobes.c

375

struct pt_regs *regs = task_pt_regs(current);

arch/x86/kernel/uprobes.c

687

struct pt_regs *regs = task_pt_regs(current);

arch/x86/kernel/uprobes.c

806

struct pt_regs *regs = task_pt_regs(current);

arch/x86/um/ptrace.c

220

void *fpregs = task_pt_regs(target)->regs.fp;

arch/x86/um/ptrace.c

231

void *fpregs = task_pt_regs(target)->regs.fp;

arch/x86/xen/smp_pv.c

253

ctxt->user_regs.esp = (unsigned long)task_pt_regs(idle);

arch/x86/xen/smp_pv.c

355

xen_cpu_bringup_again((unsigned long)task_pt_regs(current));

arch/xtensa/include/asm/processor.h

223

#define KSTK_EIP(tsk) (task_pt_regs(tsk)->pc)

arch/xtensa/include/asm/processor.h

224

#define KSTK_ESP(tsk) (task_pt_regs(tsk)->areg[1])

arch/xtensa/kernel/process.c

273

struct pt_regs *childregs = task_pt_regs(p);

arch/xtensa/kernel/ptrace.c

124

struct pt_regs *regs = task_pt_regs(target);

arch/xtensa/kernel/ptrace.c

157

struct pt_regs *regs = task_pt_regs(target);

arch/xtensa/kernel/ptrace.c

274

regs = task_pt_regs(child);

arch/xtensa/kernel/ptrace.c

338

regs = task_pt_regs(child);

arch/xtensa/kernel/ptrace.c

43

struct pt_regs *regs = task_pt_regs(target);

arch/xtensa/kernel/ptrace.c

84

regs = task_pt_regs(target);

arch/xtensa/kernel/signal.c

457

task_pt_regs(current)->icountlevel = 0;

arch/xtensa/kernel/signal.c

497

task_pt_regs(current)->icountlevel = 1;

arch/xtensa/kernel/signal.c

523

task_pt_regs(current)->icountlevel = 1;

arch/xtensa/kernel/smp.c

241

start_info.stack = (unsigned long)task_pt_regs(idle);

include/linux/elfcore.h

92

elf_core_copy_regs(elfregs, task_pt_regs(t));

include/linux/kstack_erase.h

43

return (unsigned long)task_pt_regs(tsk);

include/linux/perf_regs.h

46

regs_user->regs = task_pt_regs(current);

include/linux/ptrace.h

389

#define current_pt_regs() task_pt_regs(current)

include/uapi/linux/bpf.h

6078

FN(task_pt_regs, 175, ##ctx) \

kernel/bpf/stackmap.c

555

regs = task_pt_regs(task);

kernel/events/callchain.c

251

regs = task_pt_regs(current);

kernel/ptrace.c

1100

struct pt_regs *regs = task_pt_regs(child);

kernel/ptrace.c

997

struct pt_regs *regs = task_pt_regs(child);

kernel/seccomp.c

251

struct pt_regs *regs = task_pt_regs(task);

kernel/signal.c

1221

struct pt_regs *regs = task_pt_regs(current);

kernel/stacktrace.c

235

arch_stack_walk_user(consume_entry, &c, task_pt_regs(current));

kernel/trace/bpf_trace.c

780

return (unsigned long) task_pt_regs(task);

kernel/unwind/deferred.c

240

!user_mode(task_pt_regs(current)))

kernel/unwind/user.c

117

struct pt_regs *regs = task_pt_regs(current);

kernel/unwind/user.c

70

struct pt_regs *regs = task_pt_regs(current);

lib/syscall.c

20

regs = task_pt_regs(target);

tools/include/uapi/linux/bpf.h

6078

FN(task_pt_regs, 175, ##ctx) \