arch/arm64/kernel/mte.c
534
if (!tsk->ptrace || (current != tsk->parent) ||
arch/csky/kernel/asm-offsets.c
15
DEFINE(TASK_PTRACE, offsetof(struct task_struct, ptrace));
arch/microblaze/kernel/asm-offsets.c
75
DEFINE(TASK_PTRACE, offsetof(struct task_struct, ptrace));
arch/openrisc/kernel/asm-offsets.c
42
DEFINE(TASK_PTRACE, offsetof(struct task_struct, ptrace));
arch/powerpc/include/asm/book3s/64/kup.h
208
#include <asm/ptrace.h>
arch/riscv/kernel/ptrace.c
132
struct __riscv_v_regset_state *ptrace)
arch/riscv/kernel/ptrace.c
140
if (vstate->vlenb != ptrace->vlenb)
arch/riscv/kernel/ptrace.c
145
if (ptrace->vcsr & reserved)
arch/riscv/kernel/ptrace.c
151
if (ptrace->vtype & reserved)
arch/riscv/kernel/ptrace.c
155
vsew = (ptrace->vtype & VTYPE_VSEW) >> VTYPE_VSEW_SHIFT;
arch/riscv/kernel/ptrace.c
161
vfrac = (ptrace->vtype & VTYPE_VLMUL_FRAC);
arch/riscv/kernel/ptrace.c
162
vlmul = (ptrace->vtype & VTYPE_VLMUL);
arch/riscv/kernel/ptrace.c
173
vl = ptrace->vl ? ptrace->vl : 1;
arch/riscv/kernel/ptrace.c
191
if (ptrace->vtype & reserved)
arch/riscv/kernel/ptrace.c
198
if (ptrace->vtype & VTYPE_VEDIV_THEAD)
arch/riscv/kernel/ptrace.c
201
vsew = (ptrace->vtype & VTYPE_VSEW_THEAD) >> VTYPE_VSEW_THEAD_SHIFT;
arch/riscv/kernel/ptrace.c
204
vlmul = (ptrace->vtype & VTYPE_VLMUL_THEAD);
arch/riscv/kernel/ptrace.c
208
vl = ptrace->vl ? ptrace->vl : 1;
arch/s390/kernel/traps.c
151
if (current->ptrace)
arch/s390/kernel/traps.c
76
if (!current->ptrace)
arch/um/kernel/ptrace.c
143
int ptraced = current->ptrace;
arch/um/kernel/signal.c
56
if (test_thread_flag(TIF_SINGLESTEP) && (current->ptrace & PT_PTRACED))
arch/um/os-Linux/process.c
62
ptrace(PTRACE_KILL, pid);
arch/um/os-Linux/process.c
63
ptrace(PTRACE_CONT, pid);
arch/um/os-Linux/registers.c
24
err = ptrace(PTRACE_GETREGS, pid, 0, exec_regs);
arch/um/os-Linux/skas/mem.c
109
err = ptrace(PTRACE_CONT, pid, 0, 0);
arch/um/os-Linux/skas/process.c
129
err = ptrace(PTRACE_CONT, pid, 0, 0);
arch/um/os-Linux/skas/process.c
255
err = ptrace(PTRACE_CONT, pid, 0, SIGSEGV);
arch/um/os-Linux/skas/process.c
508
if (ptrace(PTRACE_SETOPTIONS, mm_id->pid, NULL,
arch/um/os-Linux/skas/process.c
669
if (ptrace(PTRACE_SETREGS, pid, 0, regs->gp)) {
arch/um/os-Linux/skas/process.c
686
if (ptrace(op, pid, 0, 0)) {
arch/um/os-Linux/skas/process.c
700
if (ptrace(PTRACE_GETREGS, pid, 0, regs->gp)) {
arch/um/os-Linux/skas/process.c
731
ptrace(PTRACE_GETSIGINFO, pid, 0,
arch/um/os-Linux/skas/process.c
95
if (ptrace(PTRACE_GETREGS, pid, 0, regs) < 0)
arch/um/os-Linux/start_up.c
131
if (ptrace(PTRACE_CONT, pid, 0, 0) < 0)
arch/um/os-Linux/start_up.c
150
if ((ptrace(PTRACE_SETOPTIONS, pid, 0,
arch/um/os-Linux/start_up.c
156
if (ptrace(PTRACE_SYSEMU_SINGLESTEP, pid, 0, 0) < 0)
arch/um/os-Linux/start_up.c
169
n = ptrace(PTRACE_POKEUSER, pid, PT_SYSCALL_RET_OFFSET,
arch/um/os-Linux/start_up.c
203
if ((ptrace(PTRACE_SETOPTIONS, pid, 0,
arch/um/os-Linux/start_up.c
208
if (ptrace(PTRACE_SYSCALL, pid, 0, 0) < 0)
arch/um/os-Linux/start_up.c
220
syscall = ptrace(PTRACE_PEEKUSER, pid, PT_SYSCALL_NR_OFFSET,
arch/um/os-Linux/start_up.c
223
n = ptrace(PTRACE_POKEUSER, pid, PT_SYSCALL_NR_OFFSET,
arch/um/os-Linux/start_up.c
48
ptrace(PTRACE_TRACEME, 0, 0, 0) < 0) {
arch/x86/um/os-Linux/registers.c
31
if (ptrace(PTRACE_GETREGSET, pid, ptrace_regset, &iov) < 0)
arch/x86/um/os-Linux/registers.c
43
if (ptrace(PTRACE_SETREGSET, pid, ptrace_regset, &iov) < 0)
arch/x86/um/os-Linux/registers.c
63
ret = ptrace(PTRACE_GETREGSET, pid, ptrace_regset, &iov);
arch/x86/um/os-Linux/registers.c
74
ret = ptrace(PTRACE_GETREGSET, pid, ptrace_regset, &iov);
arch/x86/um/os-Linux/tls.c
53
ret = ptrace(PTRACE_SET_THREAD_AREA, pid, info->entry_number,
arch/x86/um/os-Linux/tls.c
64
ret = ptrace(PTRACE_GET_THREAD_AREA, pid, info->entry_number,
arch/x86/um/ptrace_user.c
11
if (ptrace(PTRACE_GETREGS, pid, 0, regs_out) < 0)
arch/x86/um/ptrace_user.c
18
if (ptrace(PTRACE_SETREGS, pid, 0, regs) < 0)
arch/xtensa/kernel/asm-offsets.c
75
DEFINE(TASK_PTRACE, offsetof (struct task_struct, ptrace));
drivers/connector/cn_proc.c
247
ev->event_data.ptrace.process_pid = task->pid;
drivers/connector/cn_proc.c
248
ev->event_data.ptrace.process_tgid = task->tgid;
drivers/connector/cn_proc.c
250
ev->event_data.ptrace.tracer_pid = current->pid;
drivers/connector/cn_proc.c
251
ev->event_data.ptrace.tracer_tgid = current->tgid;
drivers/connector/cn_proc.c
253
ev->event_data.ptrace.tracer_pid = 0;
drivers/connector/cn_proc.c
254
ev->event_data.ptrace.tracer_tgid = 0;
fs/exec.c
1008
if (unlikely(leader->ptrace))
fs/exec.c
1491
if (p->ptrace)
fs/proc/base.c
888
ptrace_active = READ_ONCE(task->ptrace) &&
include/linux/ptrace.h
119
if (unlikely(task->ptrace))
include/linux/ptrace.h
135
return task->ptrace & PT_EVENT_FLAG(event);
include/linux/ptrace.h
154
if ((current->ptrace & (PT_PTRACED|PT_SEIZED)) == PT_PTRACED)
include/linux/ptrace.h
200
static inline void ptrace_init_task(struct task_struct *child, bool ptrace)
include/linux/ptrace.h
205
child->ptrace = 0;
include/linux/ptrace.h
208
if (unlikely(ptrace) && current->ptrace) {
include/linux/ptrace.h
209
child->ptrace = current->ptrace;
include/linux/ptrace.h
212
if (child->ptrace & PT_SEIZED)
include/linux/ptrace.h
409
int ptrace = current->ptrace;
include/linux/ptrace.h
412
if (!(ptrace & PT_PTRACED))
include/linux/ptrace.h
415
signr = ptrace_notify(SIGTRAP | ((ptrace & PT_TRACESYSGOOD) ? 0x80 : 0),
include/linux/ptrace.h
97
if (unlikely(child->ptrace))
include/linux/sched.h
843
unsigned int ptrace;
include/uapi/linux/cn_proc.h
133
} ptrace;
kernel/exit.c
1141
eligible_child(struct wait_opts *wo, bool ptrace, struct task_struct *p)
kernel/exit.c
1150
if (ptrace || (wo->wo_flags & __WALL))
kernel/exit.c
1299
static int *task_stopped_code(struct task_struct *p, bool ptrace)
kernel/exit.c
1301
if (ptrace) {
kernel/exit.c
1330
int ptrace, struct task_struct *p)
kernel/exit.c
1340
if (!ptrace && !(wo->wo_flags & WUNTRACED))
kernel/exit.c
1343
if (!task_stopped_code(p, ptrace))
kernel/exit.c
1349
p_code = task_stopped_code(p, ptrace);
kernel/exit.c
1375
why = ptrace ? CLD_TRAPPED : CLD_STOPPED;
kernel/exit.c
1453
static int wait_consider_task(struct wait_opts *wo, int ptrace,
kernel/exit.c
1467
ret = eligible_child(wo, ptrace, p);
kernel/exit.c
1476
if (likely(!ptrace))
kernel/exit.c
1481
if (likely(!ptrace) && unlikely(p->ptrace)) {
kernel/exit.c
1494
ptrace = 1;
kernel/exit.c
1506
if (unlikely(ptrace) || likely(!p->ptrace))
kernel/exit.c
1530
if (likely(!ptrace) || (wo->wo_flags & (WCONTINUED | WEXITED)))
kernel/exit.c
1544
ret = wait_task_stopped(wo, ptrace, p);
kernel/exit.c
1623
static bool is_effectively_child(struct wait_opts *wo, bool ptrace,
kernel/exit.c
1627
!ptrace ? target->real_parent : target->parent;
kernel/exit.c
1639
bool ptrace;
kernel/exit.c
1643
ptrace = false;
kernel/exit.c
1645
if (target && is_effectively_child(wo, ptrace, target)) {
kernel/exit.c
1646
retval = wait_consider_task(wo, ptrace, target);
kernel/exit.c
1651
ptrace = true;
kernel/exit.c
1653
if (target && target->ptrace &&
kernel/exit.c
1654
is_effectively_child(wo, ptrace, target)) {
kernel/exit.c
1655
retval = wait_consider_task(wo, ptrace, target);
kernel/exit.c
683
if (!p->ptrace &&
kernel/exit.c
714
BUG_ON((!t->ptrace) != (rcu_access_pointer(t->parent) == father));
kernel/exit.c
715
if (likely(!t->ptrace))
kernel/exit.c
750
if (unlikely(tsk->ptrace)) {
kernel/ptrace.c
1139
bool seized = child->ptrace & PT_SEIZED;
kernel/ptrace.c
120
BUG_ON(!child->ptrace);
kernel/ptrace.c
134
child->ptrace = 0;
kernel/ptrace.c
1387
SYSCALL_DEFINE4(ptrace, long, request, long, pid, unsigned long, addr,
kernel/ptrace.c
1526
COMPAT_SYSCALL_DEFINE4(ptrace, compat_long_t, request, compat_long_t, pid,
kernel/ptrace.c
251
if (child->ptrace && child->parent == current) {
kernel/ptrace.c
372
current->ptrace & PT_SUSPEND_SECCOMP)
kernel/ptrace.c
459
if (task->ptrace)
kernel/ptrace.c
462
task->ptrace = flags;
kernel/ptrace.c
493
if (!current->ptrace) {
kernel/ptrace.c
501
current->ptrace = PT_PTRACED;
kernel/ptrace.c
54
if (!tsk->ptrace ||
kernel/ptrace.c
576
WARN_ON(!child->ptrace || child->exit_state);
kernel/ptrace.c
599
if (unlikely(p->ptrace & PT_EXITKILL))
kernel/ptrace.c
669
flags = child->ptrace;
kernel/ptrace.c
672
child->ptrace = flags;
kernel/seccomp.c
1093
unlikely(current->ptrace & PT_SUSPEND_SECCOMP))
kernel/seccomp.c
1394
unlikely(current->ptrace & PT_SUSPEND_SECCOMP))
kernel/signal.c
1006
(sig == SIGKILL || !p->ptrace)) {
kernel/signal.c
121
if (t->ptrace && sig != SIGKILL)
kernel/signal.c
1318
(!t->ptrace || (handler == HANDLER_EXIT)))
kernel/signal.c
2181
WARN_ON_ONCE(!tsk->ptrace &&
kernel/signal.c
2232
if (!tsk->ptrace && sig == SIGCHLD &&
kernel/signal.c
2376
if (!current->ptrace || __fatal_signal_pending(current))
kernel/signal.c
2436
if (current->ptrace)
kernel/signal.c
2438
if (gstop_done && (!current->ptrace || ptrace_reparented(current)))
kernel/signal.c
2601
if (likely(!(t->ptrace & PT_SEIZED)))
kernel/signal.c
2609
if (likely(!current->ptrace)) {
kernel/signal.c
2673
if (current->ptrace & PT_SEIZED) {
kernel/signal.c
2919
if (unlikely(current->ptrace) && (signr != SIGKILL) &&
kernel/signal.c
550
return !tsk->ptrace;
kernel/signal.c
854
WARN_ON_ONCE(!(t->ptrace & PT_SEIZED));
kernel/signal.c
902
if (likely(!(t->ptrace & PT_SEIZED))) {
mm/nommu.c
870
if (!(prot & PROT_WRITE) && !current->ptrace)
tools/perf/arch/x86/tests/bp-modify.c
110
rip = ptrace(PTRACE_PEEKUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
119
if (ptrace(PTRACE_DETACH, child, NULL, NULL)) {
tools/perf/arch/x86/tests/bp-modify.c
154
if (ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
160
if (ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
166
if (!ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
172
if (ptrace(PTRACE_CONT, child, NULL, NULL)) {
tools/perf/arch/x86/tests/bp-modify.c
183
rip = ptrace(PTRACE_PEEKUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
193
if (ptrace(PTRACE_DETACH, child, NULL, NULL)) {
tools/perf/arch/x86/tests/bp-modify.c
40
int err = ptrace(PTRACE_TRACEME, 0, NULL, NULL);
tools/perf/arch/x86/tests/bp-modify.c
81
if (ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
87
if (ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
93
if (ptrace(PTRACE_POKEUSER, child,
tools/perf/arch/x86/tests/bp-modify.c
99
if (ptrace(PTRACE_CONT, child, NULL, NULL)) {
tools/testing/selftests/arm64/abi/ptrace.c
112
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_TLS, &write_iov);
tools/testing/selftests/arm64/abi/ptrace.c
117
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_TLS,
tools/testing/selftests/arm64/abi/ptrace.c
145
ret = ptrace(PTRACE_GETREGSET, child, type, &iov);
tools/testing/selftests/arm64/abi/ptrace.c
165
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL))
tools/testing/selftests/arm64/abi/ptrace.c
206
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &si)) {
tools/testing/selftests/arm64/abi/ptrace.c
225
if (ptrace(PTRACE_CONT, pid, NULL, sig)) {
tools/testing/selftests/arm64/abi/ptrace.c
45
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_TLS, &read_iov);
tools/testing/selftests/arm64/abi/ptrace.c
51
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_TLS, &write_iov);
tools/testing/selftests/arm64/abi/ptrace.c
55
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_TLS, &read_iov);
tools/testing/selftests/arm64/abi/ptrace.c
61
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_TLS, &read_iov);
tools/testing/selftests/arm64/abi/ptrace.c
82
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_TLS, &write_iov);
tools/testing/selftests/arm64/abi/ptrace.c
90
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_TLS, &read_iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1116
ret = ptrace(PTRACE_SETREGSET, child, NT_PRFPREG, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1146
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_FPMR, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1216
ret = ptrace(PTRACE_SETREGSET, child, regset, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1251
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_SVE, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1319
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_ZA, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
1362
ret = ptrace(PTRACE_SETREGSET, child, NT_ARM_ZT, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
230
ret = ptrace(PTRACE_TRACEME, 0, 0, 0);
tools/testing/selftests/arm64/fp/fp-ptrace.c
372
ret = ptrace(PTRACE_GETREGSET, child, NT_PRSTATUS, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
381
ret = ptrace(PTRACE_SETREGSET, child, NT_PRSTATUS, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
389
ret = ptrace(restart_type, child, 0, 0);
tools/testing/selftests/arm64/fp/fp-ptrace.c
420
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_SVE, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
504
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_SSVE, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
586
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_ZA, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
638
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_ZT, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
659
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_FPMR, &iov);
tools/testing/selftests/arm64/fp/fp-ptrace.c
678
ret = ptrace(PTRACE_GETREGSET, child, NT_PRFPREG, &iov);
tools/testing/selftests/arm64/fp/sve-ptrace.c
102
ret = ptrace(PTRACE_GETREGSET, pid, NT_PRFPREG, &iov);
tools/testing/selftests/arm64/fp/sve-ptrace.c
115
ret = ptrace(PTRACE_SETREGSET, pid, NT_PRFPREG, &iov);
tools/testing/selftests/arm64/fp/sve-ptrace.c
144
ret = ptrace(PTRACE_GETREGSET, pid, type->regset, &iov);
tools/testing/selftests/arm64/fp/sve-ptrace.c
171
ret = ptrace(PTRACE_SETREGSET, pid, type->regset, &iov);
tools/testing/selftests/arm64/fp/sve-ptrace.c
775
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &si)) {
tools/testing/selftests/arm64/fp/sve-ptrace.c
794
if (ptrace(PTRACE_CONT, pid, NULL, sig)) {
tools/testing/selftests/arm64/fp/sve-ptrace.c
84
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL))
tools/testing/selftests/arm64/fp/za-ptrace.c
104
return ptrace(PTRACE_SETREGSET, pid, NT_ARM_ZA, &iov);
tools/testing/selftests/arm64/fp/za-ptrace.c
284
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &si)) {
tools/testing/selftests/arm64/fp/za-ptrace.c
303
if (ptrace(PTRACE_CONT, pid, NULL, sig)) {
tools/testing/selftests/arm64/fp/za-ptrace.c
50
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL))
tools/testing/selftests/arm64/fp/za-ptrace.c
82
if (ptrace(PTRACE_GETREGSET, pid, NT_ARM_ZA, &iov))
tools/testing/selftests/arm64/fp/zt-ptrace.c
108
return ptrace(PTRACE_GETREGSET, pid, NT_ARM_ZT, &iov);
tools/testing/selftests/arm64/fp/zt-ptrace.c
117
return ptrace(PTRACE_SETREGSET, pid, NT_ARM_ZT, &iov);
tools/testing/selftests/arm64/fp/zt-ptrace.c
288
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &si)) {
tools/testing/selftests/arm64/fp/zt-ptrace.c
307
if (ptrace(PTRACE_CONT, pid, NULL, sig)) {
tools/testing/selftests/arm64/fp/zt-ptrace.c
45
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL))
tools/testing/selftests/arm64/fp/zt-ptrace.c
77
if (ptrace(PTRACE_GETREGSET, pid, NT_ARM_ZA, &iov))
tools/testing/selftests/arm64/fp/zt-ptrace.c
99
return ptrace(PTRACE_SETREGSET, pid, NT_ARM_ZA, &iov);
tools/testing/selftests/arm64/gcs/libc-gcs.c
158
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL))
tools/testing/selftests/arm64/gcs/libc-gcs.c
197
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &si)) {
tools/testing/selftests/arm64/gcs/libc-gcs.c
218
if (ptrace(PTRACE_CONT, pid, NULL, sig)) {
tools/testing/selftests/arm64/gcs/libc-gcs.c
232
ret = ptrace(PTRACE_GETREGSET, child, NT_ARM_GCS, &iov);
tools/testing/selftests/arm64/gcs/libc-gcs.c
254
val = ptrace(PTRACE_PEEKDATA, child, (void *)gcspr, NULL);
tools/testing/selftests/arm64/gcs/libc-gcs.c
277
ret = ptrace(PTRACE_POKEDATA, child, (void *)gcspr, NULL);
tools/testing/selftests/arm64/gcs/libc-gcs.c
282
EXPECT_EQ(0, ptrace(PTRACE_PEEKDATA, child, (void *)gcspr, NULL));
tools/testing/selftests/arm64/gcs/libc-gcs.c
285
ret = ptrace(PTRACE_POKEDATA, child, (void *)gcspr, val);
tools/testing/selftests/arm64/gcs/libc-gcs.c
290
EXPECT_EQ(val, ptrace(PTRACE_PEEKDATA, child, (void *)gcspr, NULL));
tools/testing/selftests/breakpoints/breakpoint_test.c
108
ret = ptrace(PTRACE_POKEUSER, child_pid,
tools/testing/selftests/breakpoints/breakpoint_test.c
209
ret = ptrace(PTRACE_TRACEME, 0, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
276
child_nr_tests = ptrace(PTRACE_PEEKDATA, child_pid,
tools/testing/selftests/breakpoints/breakpoint_test.c
280
if (ptrace(PTRACE_POKEDATA, child_pid, &trapped, 1))
tools/testing/selftests/breakpoints/breakpoint_test.c
299
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
321
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
377
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
381
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
384
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/breakpoints/breakpoint_test.c
46
ret = ptrace(PTRACE_POKEUSER, child_pid,
tools/testing/selftests/breakpoints/breakpoint_test.c
88
dr7 = ptrace(PTRACE_PEEKUSER, child_pid,
tools/testing/selftests/breakpoints/breakpoint_test_arm64.c
146
if (ptrace(PTRACE_CONT, pid, NULL, NULL) < 0) {
tools/testing/selftests/breakpoints/breakpoint_test_arm64.c
173
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &siginfo) != 0) {
tools/testing/selftests/breakpoints/breakpoint_test_arm64.c
37
if (ptrace(PTRACE_TRACEME, 0, NULL, NULL) != 0) {
tools/testing/selftests/breakpoints/breakpoint_test_arm64.c
98
if (ptrace(PTRACE_SETREGSET, pid, NT_ARM_HW_WATCH, &iov) == 0)
tools/testing/selftests/breakpoints/step_after_suspend_test.c
110
if (ptrace(PTRACE_CONT, pid, NULL, NULL) < 0) {
tools/testing/selftests/breakpoints/step_after_suspend_test.c
36
if (ptrace(PTRACE_TRACEME, 0, NULL, NULL) != 0) {
tools/testing/selftests/breakpoints/step_after_suspend_test.c
78
if (ptrace(PTRACE_SINGLESTEP, pid, NULL, NULL) < 0) {
tools/testing/selftests/cgroup/test_freezer.c
607
if (ptrace(PTRACE_SEIZE, pid, NULL, NULL))
tools/testing/selftests/cgroup/test_freezer.c
610
if (ptrace(PTRACE_INTERRUPT, pid, NULL, NULL))
tools/testing/selftests/cgroup/test_freezer.c
622
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &siginfo))
tools/testing/selftests/cgroup/test_freezer.c
625
if (ptrace(PTRACE_DETACH, pid, NULL, NULL))
tools/testing/selftests/cgroup/test_freezer.c
727
if (ptrace(PTRACE_SEIZE, pid, NULL, NULL))
tools/testing/selftests/cgroup/test_freezer.c
730
if (ptrace(PTRACE_INTERRUPT, pid, NULL, NULL))
tools/testing/selftests/cgroup/test_freezer.c
748
if (ptrace(PTRACE_GETSIGINFO, pid, NULL, &siginfo))
tools/testing/selftests/cgroup/test_freezer.c
751
if (ptrace(PTRACE_DETACH, pid, NULL, NULL))
tools/testing/selftests/connector/proc_filter.c
188
event->event_data.ptrace.process_pid,
tools/testing/selftests/connector/proc_filter.c
189
event->event_data.ptrace.process_tgid,
tools/testing/selftests/connector/proc_filter.c
190
event->event_data.ptrace.tracer_pid,
tools/testing/selftests/connector/proc_filter.c
191
event->event_data.ptrace.tracer_tgid);
tools/testing/selftests/landlock/ptrace_test.c
200
ret = ptrace(PTRACE_ATTACH, parent, NULL, 0);
tools/testing/selftests/landlock/ptrace_test.c
210
ASSERT_EQ(0, ptrace(PTRACE_DETACH, parent, NULL, 0));
tools/testing/selftests/landlock/ptrace_test.c
214
ret = ptrace(PTRACE_TRACEME);
tools/testing/selftests/landlock/ptrace_test.c
256
ASSERT_EQ(0, ptrace(PTRACE_DETACH, child, NULL, 0));
tools/testing/selftests/landlock/ptrace_test.c
259
EXPECT_EQ(-1, ptrace(PTRACE_DETACH, child, NULL, 0));
tools/testing/selftests/landlock/ptrace_test.c
272
ret = ptrace(PTRACE_ATTACH, child, NULL, 0);
tools/testing/selftests/landlock/ptrace_test.c
283
ASSERT_EQ(0, ptrace(PTRACE_DETACH, child, NULL, 0));
tools/testing/selftests/landlock/ptrace_test.c
375
EXPECT_EQ(-1, ptrace(PTRACE_TRACEME));
tools/testing/selftests/landlock/ptrace_test.c
412
EXPECT_EQ(-1, ptrace(PTRACE_DETACH, child, NULL, 0));
tools/testing/selftests/landlock/ptrace_test.c
416
EXPECT_EQ(-1, ptrace(PTRACE_ATTACH, child, NULL, 0));
tools/testing/selftests/mm/memfd_secret.c
162
ret = ptrace(PTRACE_ATTACH, ppid, 0, 0);
tools/testing/selftests/mm/memfd_secret.c
175
if (ptrace(PTRACE_PEEKDATA, ppid, mem, 0))
tools/testing/selftests/mm/protection_keys.c
1325
ret = ptrace(PTRACE_ATTACH, child_pid, ignored, ignored);
tools/testing/selftests/mm/protection_keys.c
1351
ret = ptrace(PTRACE_PEEKDATA, child_pid, ptr, ignored);
tools/testing/selftests/mm/protection_keys.c
1361
ret = ptrace(PTRACE_PEEKDATA, child_pid, plain_ptr, ignored);
tools/testing/selftests/mm/protection_keys.c
1368
ret = ptrace(PTRACE_DETACH, child_pid, ignored, 0);
tools/testing/selftests/mm/protection_keys.c
1501
ptrace(PTRACE_TRACEME, 0, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1534
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1542
ret = ptrace(PTRACE_SETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1547
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1552
ret = ptrace(PTRACE_CONT, child, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1562
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1570
ret = ptrace(PTRACE_SETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1575
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1579
ret = ptrace(PTRACE_CONT, child, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1589
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_X86_XSTATE, &iov);
tools/testing/selftests/mm/protection_keys.c
1593
ret = ptrace(PTRACE_CONT, child, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1619
ptrace(PTRACE_TRACEME, 0, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1642
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_ARM_POE, &iov);
tools/testing/selftests/mm/protection_keys.c
1648
ret = ptrace(PTRACE_SETREGSET, child, (void *)NT_ARM_POE, &iov);
tools/testing/selftests/mm/protection_keys.c
1653
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_ARM_POE, &iov);
tools/testing/selftests/mm/protection_keys.c
1658
ret = ptrace(PTRACE_CONT, child, 0, 0);
tools/testing/selftests/mm/protection_keys.c
1668
ret = ptrace(PTRACE_GETREGSET, child, (void *)NT_ARM_POE, &iov);
tools/testing/selftests/mm/protection_keys.c
1672
ret = ptrace(PTRACE_CONT, child, 0, 0);
tools/testing/selftests/nolibc/nolibc-test.c
1463
CASE_TEST(ptrace); EXPECT_SYSER(1, ptrace(PTRACE_CONT, getpid(), NULL, NULL), -1, ESRCH); break;
tools/testing/selftests/powerpc/ptrace/perf-hwbreak.c
816
int ret = ptrace(PTRACE_TRACEME, 0, NULL, 0);
tools/testing/selftests/powerpc/ptrace/perf-hwbreak.c
828
if (ptrace(PPC_PTRACE_GETHWDBGINFO, child_pid, NULL, &dbginfo)) {
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
121
if (ptrace(PTRACE_TRACEME, 0, NULL, 0)) {
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
224
ptrace(PTRACE_GETSIGINFO, child_pid, NULL, &siginfo);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
241
ptrace(PTRACE_SINGLESTEP, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
248
if (ptrace(PTRACE_SET_DEBUGREG, child_pid, 0, wp_addr)) {
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
256
int wh = ptrace(PPC_PTRACE_SETHWDEBUG, child_pid, 0, info);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
267
if (ptrace(PPC_PTRACE_DELHWDEBUG, child_pid, 0, wh) < 0) {
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
289
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
299
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
310
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
329
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
362
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
369
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
376
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
392
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
410
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
419
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
428
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
455
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
458
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
486
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
489
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
509
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
518
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
527
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
54
if (ptrace(PPC_PTRACE_GETHWDBGINFO, child_pid, NULL, dbginfo)) {
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
546
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
564
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-hwbreak.c
612
ptrace(PTRACE_CONT, child_pid, NULL, 0);
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
127
if (ptrace(PTRACE_SETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
130
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
134
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
170
if (ptrace(PTRACE_SETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
173
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
177
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
203
if (ptrace(PTRACE_CONT, chld, 0, 0) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
74
if (ptrace(PTRACE_TRACEME, 0, 0, 0) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
92
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace-syscall.c
96
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/powerpc/ptrace/ptrace.h
116
ret = ptrace(PTRACE_GETREGSET, child, type, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
136
ret = ptrace(PTRACE_SETREGSET, child, type, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
158
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TAR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
166
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_PPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
174
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_DSCR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
206
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TAR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
213
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_PPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
220
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_DSCR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
248
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CTAR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
256
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CPPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
264
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CDSCR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
297
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CTAR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
304
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CPPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
311
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CDSCR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
331
ret = ptrace(PTRACE_GETFPREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
350
ret = ptrace(PTRACE_GETFPREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
359
ret = ptrace(PTRACE_SETFPREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
377
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CFPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
401
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CFPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
410
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CFPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
430
ret = ptrace(PTRACE_GETREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
519
ret = ptrace(PTRACE_GETREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
528
ret = ptrace(PTRACE_SETREGS, child, NULL, regs);
tools/testing/selftests/powerpc/ptrace/ptrace.h
551
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CGPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
579
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CGPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
588
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CGPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
601
ret = ptrace(PTRACE_GETVRREGS, child, 0, vmx);
tools/testing/selftests/powerpc/ptrace/ptrace.h
617
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CVMX, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
631
ret = ptrace(PTRACE_SETVRREGS, child, 0, vmx);
tools/testing/selftests/powerpc/ptrace/ptrace.h
648
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CVMX, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
661
ret = ptrace(PTRACE_GETVSRREGS, child, 0, vsx);
tools/testing/selftests/powerpc/ptrace/ptrace.h
677
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_CVSX, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
68
ret = ptrace(PTRACE_ATTACH, child, NULL, NULL);
tools/testing/selftests/powerpc/ptrace/ptrace.h
690
ret = ptrace(PTRACE_SETVSRREGS, child, 0, vsx);
tools/testing/selftests/powerpc/ptrace/ptrace.h
707
ret = ptrace(PTRACE_SETREGSET, child, NT_PPC_TM_CVSX, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
731
ret = ptrace(PTRACE_GETREGSET, child, NT_PPC_TM_SPR, &iov);
tools/testing/selftests/powerpc/ptrace/ptrace.h
85
ret = ptrace(PTRACE_DETACH, child, NULL, NULL);
tools/testing/selftests/powerpc/ptrace/ptrace.h
97
ret = ptrace(PTRACE_CONT, child, NULL, NULL);
tools/testing/selftests/proc/proc-empty-vm.c
467
rv = ptrace(PTRACE_TRACEME, 0, NULL, NULL);
tools/testing/selftests/ptrace/vmaccess.c
20
ptrace(PTRACE_TRACEME, 0, 0L, 0L);
tools/testing/selftests/ptrace/vmaccess.c
59
k = ptrace(PTRACE_ATTACH, pid, 0L, 0L);
tools/testing/selftests/ptrace/vmaccess.c
69
k = ptrace(PTRACE_ATTACH, pid, 0L, 0L);
tools/testing/selftests/ptrace/vmaccess.c
75
k = ptrace(PTRACE_DETACH, pid, 0L, 0L);
tools/testing/selftests/riscv/cfi/cfitests.c
114
ret = ptrace(PTRACE_SETREGSET, pid, (void *)NT_RISCV_USER_CFI, &iov);
tools/testing/selftests/riscv/cfi/cfitests.c
122
ptrace(PTRACE_CONT, pid, NULL, NULL);
tools/testing/selftests/riscv/cfi/cfitests.c
48
long ptrace(int request, pid_t pid, void *addr, void *data);
tools/testing/selftests/riscv/cfi/cfitests.c
68
ptrace(PTRACE_TRACEME, 0, NULL, NULL);
tools/testing/selftests/riscv/cfi/cfitests.c
89
ret = ptrace(PTRACE_GETREGSET, pid, (void *)NT_RISCV_USER_CFI, &iov);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
154
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
160
ASSERT_EQ(0, ptrace(PTRACE_POKEDATA, pid, &chld_lock, 0));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
164
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
171
vstart_csr = ptrace(PTRACE_PEEKDATA, pid, &vstart, NULL);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
175
vl_csr = ptrace(PTRACE_PEEKDATA, pid, &vl, NULL);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
179
vtype_csr = ptrace(PTRACE_PEEKDATA, pid, &vtype, NULL);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
183
vcsr_csr = ptrace(PTRACE_PEEKDATA, pid, &vcsr, NULL);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
187
vlenb_csr = ptrace(PTRACE_PEEKDATA, pid, &vlenb, NULL);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
198
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
267
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
273
ASSERT_EQ(0, ptrace(PTRACE_POKEDATA, pid, &chld_lock, 0));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
277
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
289
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
309
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
311
ASSERT_EQ(0, ptrace(PTRACE_SETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
313
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
322
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
47
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
53
ASSERT_EQ(0, ptrace(PTRACE_POKEDATA, pid, &chld_lock, 0));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
57
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
597
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
603
ASSERT_EQ(0, ptrace(PTRACE_POKEDATA, pid, &chld_lock, 0));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
607
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
619
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
646
ret = ptrace(PTRACE_SETREGSET, pid, NT_RISCV_VECTOR, &iov);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
72
ret = ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov);
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
806
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
812
ASSERT_EQ(0, ptrace(PTRACE_POKEDATA, pid, &chld_lock, 0));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
816
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
828
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
854
ASSERT_EQ(0, ptrace(PTRACE_SETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
861
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
863
ASSERT_EQ(0, ptrace(PTRACE_SETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
865
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
874
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
889
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
891
ASSERT_EQ(0, ptrace(PTRACE_SETREGSET, pid, NT_PRSTATUS, &iov));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
893
ASSERT_EQ(0, ptrace(PTRACE_CONT, pid, NULL, NULL));
tools/testing/selftests/riscv/vector/validate_v_ptrace.c
902
ASSERT_EQ(0, ptrace(PTRACE_GETREGSET, pid, NT_RISCV_VECTOR, &iov));
tools/testing/selftests/riscv/vector/vstate_ptrace.c
105
ptrace(PTRACE_CONT, child, NULL, NULL);
tools/testing/selftests/riscv/vector/vstate_ptrace.c
21
return ptrace(op, pid, type, &v_iovec);
tools/testing/selftests/riscv/vector/vstate_ptrace.c
28
if (ptrace(PTRACE_TRACEME, -1, NULL, NULL)) {
tools/testing/selftests/seccomp/seccomp_bpf.c
1549
ret = ptrace(PTRACE_ATTACH, tracee, NULL, 0);
tools/testing/selftests/seccomp/seccomp_bpf.c
1556
ret = ptrace(PTRACE_SETOPTIONS, tracee, NULL, ptrace_syscall ?
tools/testing/selftests/seccomp/seccomp_bpf.c
1563
ret = ptrace(ptrace_syscall ? PTRACE_SYSCALL : PTRACE_CONT,
tools/testing/selftests/seccomp/seccomp_bpf.c
1596
ret = ptrace(ptrace_syscall ? PTRACE_SYSCALL : PTRACE_CONT,
tools/testing/selftests/seccomp/seccomp_bpf.c
1658
ret = ptrace(PTRACE_GETEVENTMSG, tracee, NULL, &msg);
tools/testing/selftests/seccomp/seccomp_bpf.c
1669
ret = ptrace(PTRACE_POKEDATA, tracee, info->poke_addr, 0x1001);
tools/testing/selftests/seccomp/seccomp_bpf.c
1758
EXPECT_EQ(0, ptrace(PTRACE_SET_SYSCALL, tracee, NULL, _nr))
tools/testing/selftests/seccomp/seccomp_bpf.c
1772
EXPECT_EQ(0, ptrace(PTRACE_SETREGSET, tracee, \
tools/testing/selftests/seccomp/seccomp_bpf.c
1934
# define ARCH_GETREGS(_regs) ptrace(PTRACE_GETREGS, tracee, 0, &(_regs))
tools/testing/selftests/seccomp/seccomp_bpf.c
1935
# define ARCH_SETREGS(_regs) ptrace(PTRACE_SETREGS, tracee, 0, &(_regs))
tools/testing/selftests/seccomp/seccomp_bpf.c
1941
ptrace(PTRACE_GETREGSET, tracee, NT_PRSTATUS, &__v); \
tools/testing/selftests/seccomp/seccomp_bpf.c
1947
ptrace(PTRACE_SETREGSET, tracee, NT_PRSTATUS, &__v); \
tools/testing/selftests/seccomp/seccomp_bpf.c
2017
ret = ptrace(PTRACE_GETEVENTMSG, tracee, NULL, &msg);
tools/testing/selftests/seccomp/seccomp_bpf.c
2078
ret = ptrace(PTRACE_GETEVENTMSG, tracee, NULL, &msg);
tools/testing/selftests/seccomp/seccomp_bpf.c
2135
FIXTURE_VARIANT_ADD(TRACE_syscall, ptrace) {
tools/testing/selftests/seccomp/seccomp_bpf.c
3069
EXPECT_EQ(0, ptrace(PTRACE_TRACEME));
tools/testing/selftests/seccomp/seccomp_bpf.c
3114
ASSERT_EQ(0, ptrace(PTRACE_SETOPTIONS, child_pid, NULL,
tools/testing/selftests/seccomp/seccomp_bpf.c
3116
ASSERT_EQ(0, ptrace(PTRACE_CONT, child_pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
3124
ASSERT_EQ(0, ptrace(PTRACE_GETEVENTMSG, child_pid, NULL, &msg));
tools/testing/selftests/seccomp/seccomp_bpf.c
3130
ASSERT_EQ(0, ptrace(PTRACE_GETSIGINFO, child_pid, NULL, &info));
tools/testing/selftests/seccomp/seccomp_bpf.c
3140
ASSERT_EQ(0, ptrace(PTRACE_CONT, child_pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
3144
ASSERT_EQ(0, ptrace(PTRACE_GETSIGINFO, child_pid, NULL, &info));
tools/testing/selftests/seccomp/seccomp_bpf.c
3155
ASSERT_EQ(0, ptrace(PTRACE_CONT, child_pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
3159
ASSERT_EQ(0, ptrace(PTRACE_CONT, child_pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
3166
ASSERT_EQ(0, ptrace(PTRACE_GETEVENTMSG, child_pid, NULL, &msg));
tools/testing/selftests/seccomp/seccomp_bpf.c
3189
ASSERT_EQ(0, ptrace(PTRACE_CONT, child_pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
3334
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, pid));
tools/testing/selftests/seccomp/seccomp_bpf.c
3341
ret = ptrace(PTRACE_SECCOMP_GET_METADATA, pid, sizeof(md), &md);
tools/testing/selftests/seccomp/seccomp_bpf.c
3351
ret = ptrace(PTRACE_SECCOMP_GET_METADATA, pid, sizeof(md), &md);
tools/testing/selftests/seccomp/seccomp_bpf.c
4463
ASSERT_EQ(0, ptrace(PTRACE_ATTACH, self->pid, NULL, 0));
tools/testing/selftests/seccomp/seccomp_bpf.c
4465
ASSERT_EQ(-1, ptrace(PTRACE_SETOPTIONS, self->pid, NULL, PTRACE_O_SUSPEND_SECCOMP));
tools/testing/selftests/seccomp/seccomp_bpf.c
4475
ret = ptrace(PTRACE_SEIZE, self->pid, NULL, PTRACE_O_SUSPEND_SECCOMP);
tools/testing/selftests/vDSO/vdso_test_getrandom.c
262
ksft_assert(ptrace(PTRACE_TRACEME, 0, NULL, NULL) == 0);
tools/testing/selftests/vDSO/vdso_test_getrandom.c
277
ksft_assert(ptrace(PTRACE_SETOPTIONS, child, 0, PTRACE_O_TRACESYSGOOD) == 0);
tools/testing/selftests/vDSO/vdso_test_getrandom.c
279
ksft_assert(ptrace(PTRACE_GET_SYSCALL_INFO, child, sizeof(info), &info) > 0);
tools/testing/selftests/vDSO/vdso_test_getrandom.c
284
ksft_assert(ptrace(PTRACE_SYSCALL, child, 0, 0) == 0);
tools/testing/selftests/x86/fsgsbase.c
443
if (ptrace(PTRACE_TRACEME, 0, NULL, NULL) != 0)
tools/testing/selftests/x86/fsgsbase.c
458
base = ptrace(PTRACE_PEEKUSER, child, base_offset, NULL);
tools/testing/selftests/x86/fsgsbase.c
469
if (ptrace(PTRACE_POKEUSER, child, gs_offset, 0x7) != 0)
tools/testing/selftests/x86/fsgsbase.c
473
base = ptrace(PTRACE_PEEKUSER, child, base_offset, NULL);
tools/testing/selftests/x86/fsgsbase.c
483
ptrace(PTRACE_CONT, child, NULL, NULL);
tools/testing/selftests/x86/fsgsbase.c
503
if (ptrace(PTRACE_TRACEME, 0, NULL, NULL) != 0)
tools/testing/selftests/x86/fsgsbase.c
517
gs = ptrace(PTRACE_PEEKUSER, child, gs_offset, NULL);
tools/testing/selftests/x86/fsgsbase.c
525
if (ptrace(PTRACE_POKEUSER, child, base_offset, 0xFF) != 0)
tools/testing/selftests/x86/fsgsbase.c
528
gs = ptrace(PTRACE_PEEKUSER, child, gs_offset, NULL);
tools/testing/selftests/x86/fsgsbase.c
529
base = ptrace(PTRACE_PEEKUSER, child, base_offset, NULL);
tools/testing/selftests/x86/fsgsbase.c
563
ptrace(PTRACE_CONT, child, NULL, NULL);
tools/testing/selftests/x86/fsgsbase_restore.c
161
if (ptrace(PTRACE_TRACEME, 0, 0, 0) != 0)
tools/testing/selftests/x86/fsgsbase_restore.c
189
if (ptrace(PTRACE_GETREGS, chld, NULL, ®s) != 0)
tools/testing/selftests/x86/fsgsbase_restore.c
207
if (ptrace(PTRACE_SETREGS, chld, NULL, ®s2) != 0)
tools/testing/selftests/x86/fsgsbase_restore.c
209
if (ptrace(PTRACE_CONT, chld, NULL, NULL) != 0)
tools/testing/selftests/x86/fsgsbase_restore.c
217
if (ptrace(PTRACE_SETREGS, chld, NULL, ®s) != 0)
tools/testing/selftests/x86/fsgsbase_restore.c
219
if (ptrace(PTRACE_DETACH, chld, NULL, NULL) != 0)
tools/testing/selftests/x86/mov_ss_trap.c
73
if (ptrace(PTRACE_ATTACH, parent, NULL, NULL) != 0)
tools/testing/selftests/x86/mov_ss_trap.c
79
if (ptrace(PTRACE_POKEUSER, parent, (void *)offsetof(struct user, u_debugreg[0]), dr0) != 0)
tools/testing/selftests/x86/mov_ss_trap.c
82
if (ptrace(PTRACE_POKEUSER, parent, (void *)offsetof(struct user, u_debugreg[1]), dr1) != 0)
tools/testing/selftests/x86/mov_ss_trap.c
85
if (ptrace(PTRACE_POKEUSER, parent, (void *)offsetof(struct user, u_debugreg[7]), dr7) != 0)
tools/testing/selftests/x86/mov_ss_trap.c
90
if (ptrace(PTRACE_DETACH, parent, NULL, NULL) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
163
if (ptrace(PTRACE_TRACEME, 0, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
184
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
188
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
212
if (ptrace(PTRACE_SETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
215
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
219
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
244
if (ptrace(PTRACE_SETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
247
if (ptrace(PTRACE_SYSEMU, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
251
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
263
if (ptrace(PTRACE_CONT, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
283
if (ptrace(PTRACE_TRACEME, 0, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
305
if (ptrace(PTRACE_SYSCALL, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
311
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
329
if (ptrace(PTRACE_SYSCALL, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
333
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
348
if (ptrace(PTRACE_SETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
352
if (ptrace(PTRACE_CONT, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
365
if (ptrace(PTRACE_SYSCALL, chld, 0, 0) != 0)
tools/testing/selftests/x86/ptrace_syscall.c
371
if (ptrace(PTRACE_GETREGS, chld, 0, ®s) != 0)
tools/testing/selftests/x86/syscall_numbering.c
340
if (ptrace(PTRACE_TRACEME, 0, 0, 0)) {
tools/testing/selftests/x86/syscall_numbering.c
363
ptrace(PTRACE_GETREGS, testpid, NULL, ®s);
tools/testing/selftests/x86/syscall_numbering.c
394
ptrace(PTRACE_SETREGS, testpid, NULL, ®s);
tools/testing/selftests/x86/syscall_numbering.c
413
!ptrace(PTRACE_SYSCALL, testpid, NULL, NULL));
tools/testing/selftests/x86/syscall_numbering.c
415
ptrace(PTRACE_DETACH, testpid, NULL, NULL);
tools/testing/selftests/x86/test_shadow_stack.c
902
ptrace(PTRACE_TRACEME, NULL, NULL, NULL);
tools/testing/selftests/x86/test_shadow_stack.c
914
if (ptrace(PTRACE_GETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
927
if (!ptrace(PTRACE_SETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
933
if (!ptrace(PTRACE_SETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
939
if (!ptrace(PTRACE_SETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
945
if (!ptrace(PTRACE_SETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
956
if (ptrace(PTRACE_SETREGSET, pid, NT_X86_SHSTK, &iov)) {
tools/testing/selftests/x86/test_shadow_stack.c
961
if (ptrace(PTRACE_DETACH, pid, NULL, NULL)) {
tools/testing/selftests/x86/test_syscall_vdso.c
350
if (ptrace(PTRACE_TRACEME, 0L, 0L, 0L) != 0)
tools/testing/selftests/x86/test_syscall_vdso.c
372
ptrace(PTRACE_SYSCALL, pid, 0L, 0L /*sig*/);
tools/testing/selftests/x86/xstate.c
293
if (ptrace(PTRACE_GETREGSET, target, (uint32_t)NT_X86_XSTATE, &iov))
tools/testing/selftests/x86/xstate.c
301
if (ptrace(PTRACE_SETREGSET, target, (uint32_t)NT_X86_XSTATE, &iov))
tools/testing/selftests/x86/xstate.c
304
if (ptrace(PTRACE_GETREGSET, target, (uint32_t)NT_X86_XSTATE, &iov))
tools/testing/selftests/x86/xstate.c
330
if (ptrace(PTRACE_TRACEME, 0, NULL, NULL))
tools/testing/selftests/x86/xstate.c
345
ptrace(PTRACE_DETACH, child, NULL, NULL);
