arch/arc/kernel/ptrace.c

252

return membuf_write(&to, &regs->r30, sizeof(struct user_regs_arcv2));

arch/arc/kernel/ptrace.c

255

membuf_write(&to, &regs->r30, 4); /* r30 only */

arch/arm/kernel/ptrace.c

548

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

arch/arm/kernel/ptrace.c

576

return membuf_write(&to, &task_thread_info(target)->fpstate,

arch/arm/kernel/ptrace.c

621

membuf_write(&to, vfp->fpregs, sizeof(vfp->fpregs));

arch/arm64/kernel/ptrace.c

1104

membuf_write(&to, &header, sizeof(header));

arch/arm64/kernel/ptrace.c

1116

membuf_write(&to, target->thread.sme_state, end - start);

arch/arm64/kernel/ptrace.c

1226

membuf_write(&to, thread_zt_state(&target->thread),

arch/arm64/kernel/ptrace.c

1289

return membuf_write(&to, &uregs, sizeof(uregs));

arch/arm64/kernel/ptrace.c

1301

return membuf_write(&to, &enabled_keys, sizeof(enabled_keys));

arch/arm64/kernel/ptrace.c

1370

return membuf_write(&to, &user_keys, sizeof(user_keys));

arch/arm64/kernel/ptrace.c

1419

return membuf_write(&to, &user_keys, sizeof(user_keys));

arch/arm64/kernel/ptrace.c

1456

return membuf_write(&to, &ctrl, sizeof(ctrl));

arch/arm64/kernel/ptrace.c

1490

return membuf_write(&to, &target->thread.por_el0,

arch/arm64/kernel/ptrace.c

1548

return membuf_write(&to, &user_gcs, sizeof(user_gcs));

arch/arm64/kernel/ptrace.c

1911

membuf_write(&to, uregs, VFP_STATE_SIZE - sizeof(compat_ulong_t));

arch/arm64/kernel/ptrace.c

488

membuf_write(&to, &info, sizeof(info));

arch/arm64/kernel/ptrace.c

560

return membuf_write(&to, uregs, sizeof(*uregs));

arch/arm64/kernel/ptrace.c

601

return membuf_write(&to, uregs, sizeof(*uregs));

arch/arm64/kernel/ptrace.c

830

membuf_write(&to, &header, sizeof(header));

arch/arm64/kernel/ptrace.c

849

membuf_write(&to, target->thread.sve_state, end - start);

arch/arm64/kernel/ptrace.c

861

membuf_write(&to, &target->thread.uw.fpsimd_state.fpsr,

arch/csky/kernel/ptrace.c

131

return membuf_write(&to, &tmp, sizeof(tmp));

arch/csky/kernel/ptrace.c

133

return membuf_write(&to, regs, sizeof(*regs));

arch/csky/kernel/ptrace.c

86

return membuf_write(&to, regs, sizeof(*regs));

arch/hexagon/kernel/ptrace.c

48

membuf_write(&to, &regs->r00, 32*sizeof(unsigned long));

arch/loongarch/kernel/ptrace.c

123

return membuf_write(to, &target->thread.fpu.fpr,

arch/loongarch/kernel/ptrace.c

135

r = membuf_write(to, &fpr_val, sizeof(elf_fpreg_t));

arch/loongarch/kernel/ptrace.c

158

r = membuf_write(&to, &target->thread.fpu.fcc, sizeof(target->thread.fpu.fcc));

arch/loongarch/kernel/ptrace.c

159

r = membuf_write(&to, &target->thread.fpu.fcsr, sizeof(target->thread.fpu.fcsr));

arch/loongarch/kernel/ptrace.c

239

r = membuf_write(&to, &cfg_val, sizeof(u32));

arch/loongarch/kernel/ptrace.c

271

membuf_write(to, &target->thread.fpu.fpr[i], cp_sz);

arch/loongarch/kernel/ptrace.c

299

membuf_write(&to, &target->thread.fpu.fpr, wr_size);

arch/loongarch/kernel/ptrace.c

349

r = membuf_write(&to, &target->thread.lbt.scr0, sizeof(target->thread.lbt.scr0));

arch/loongarch/kernel/ptrace.c

350

r = membuf_write(&to, &target->thread.lbt.scr1, sizeof(target->thread.lbt.scr1));

arch/loongarch/kernel/ptrace.c

351

r = membuf_write(&to, &target->thread.lbt.scr2, sizeof(target->thread.lbt.scr2));

arch/loongarch/kernel/ptrace.c

352

r = membuf_write(&to, &target->thread.lbt.scr3, sizeof(target->thread.lbt.scr3));

arch/loongarch/kernel/ptrace.c

353

r = membuf_write(&to, &target->thread.lbt.eflags, sizeof(u32));

arch/loongarch/kernel/ptrace.c

354

r = membuf_write(&to, &target->thread.fpu.ftop, sizeof(u32));

arch/loongarch/kernel/ptrace.c

691

membuf_write(&to, &info, sizeof(info));

arch/loongarch/kernel/ptrace.c

82

r = membuf_write(&to, &regs->regs, sizeof(u64) * GPR_NUM);

arch/loongarch/kernel/ptrace.c

83

r = membuf_write(&to, &regs->orig_a0, sizeof(u64));

arch/loongarch/kernel/ptrace.c

84

r = membuf_write(&to, &regs->csr_era, sizeof(u64));

arch/loongarch/kernel/ptrace.c

85

r = membuf_write(&to, &regs->csr_badvaddr, sizeof(u64));

arch/m68k/kernel/ptrace.c

310

return membuf_write(&to, uregs, sizeof(uregs));

arch/mips/kernel/ptrace.c

225

return membuf_write(&to, uregs, sizeof(uregs));

arch/mips/kernel/ptrace.c

290

return membuf_write(&to, uregs, sizeof(uregs));

arch/mips/kernel/ptrace.c

416

membuf_write(to, &target->thread.fpu,

arch/mips/kernel/ptrace.c

449

membuf_write(&to, &target->thread.fpu.fcr31, sizeof(u32));

arch/mips/kernel/ptrace.c

450

membuf_write(&to, &boot_cpu_data.fpu_id, sizeof(u32));

arch/mips/kernel/ptrace.c

616

membuf_write(to, &target->thread.fpu.fpr[i], cp_sz);

arch/mips/kernel/ptrace.c

642

membuf_write(&to, &target->thread.fpu.fpr, wr_size);

arch/mips/kernel/ptrace.c

649

return membuf_write(&to, &ctrl_regs, sizeof(ctrl_regs));

arch/mips/kernel/ptrace.c

715

return membuf_write(&to, dspregs, sizeof(dspregs));

arch/mips/kernel/ptrace.c

781

return membuf_write(&to, dspregs, sizeof(dspregs));

arch/nios2/kernel/ptrace.c

29

membuf_write(&to, &regs->r1, 7 * 4); // R1..R7

arch/nios2/kernel/ptrace.c

30

membuf_write(&to, &regs->r8, 8 * 4); // R8..R15

arch/nios2/kernel/ptrace.c

31

membuf_write(&to, sw, 8 * 4); // R16..R23

arch/openrisc/kernel/ptrace.c

56

membuf_write(&to, regs->gpr + 1, 31 * 4);

arch/parisc/kernel/ptrace.c

408

return membuf_write(&to, regs->fr, ELF_NFPREG * sizeof(__u64));

arch/powerpc/kernel/ptrace/ptrace-altivec.c

56

membuf_write(&to, &target->thread.vr_state, 33 * sizeof(vector128));

arch/powerpc/kernel/ptrace/ptrace-altivec.c

62

return membuf_write(&to, &vrsave, sizeof(vrsave));

arch/powerpc/kernel/ptrace/ptrace-novsx.c

30

return membuf_write(&to, &target->thread.fp_state, 33 * sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-novsx.c

32

return membuf_write(&to, &empty_zero_page, 33 * sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-spe.c

30

membuf_write(&to, &target->thread.evr, sizeof(target->thread.evr));

arch/powerpc/kernel/ptrace/ptrace-spe.c

35

return membuf_write(&to, &target->thread.acc,

arch/powerpc/kernel/ptrace/ptrace-tm.c

104

membuf_write(&to, &target->thread.ckpt_regs, sizeof(struct user_pt_regs));

arch/powerpc/kernel/ptrace/ptrace-tm.c

249

return membuf_write(&to, buf, sizeof(buf));

arch/powerpc/kernel/ptrace/ptrace-tm.c

362

membuf_write(&to, &target->thread.ckvr_state, 33 * sizeof(vector128));

arch/powerpc/kernel/ptrace/ptrace-tm.c

368

return membuf_write(&to, &vrsave, sizeof(vrsave));

arch/powerpc/kernel/ptrace/ptrace-tm.c

489

return membuf_write(&to, buf, 32 * sizeof(double));

arch/powerpc/kernel/ptrace/ptrace-tm.c

591

membuf_write(&to, &target->thread.tm_tfhar, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-tm.c

593

membuf_write(&to, &target->thread.tm_texasr, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-tm.c

595

return membuf_write(&to, &target->thread.tm_tfiar, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-tm.c

673

return membuf_write(&to, &target->thread.tm_tar, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-tm.c

714

return membuf_write(&to, &target->thread.tm_ppr, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-tm.c

754

return membuf_write(&to, &target->thread.tm_dscr, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-view.c

228

membuf_write(&to, target->thread.regs, sizeof(struct user_pt_regs));

arch/powerpc/kernel/ptrace/ptrace-view.c

296

return membuf_write(&to, &target->thread.regs->ppr, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-view.c

313

return membuf_write(&to, &target->thread.dscr, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-view.c

327

return membuf_write(&to, &target->thread.tar, sizeof(u64));

arch/powerpc/kernel/ptrace/ptrace-view.c

361

return membuf_write(&to, &target->thread.ebbrr, 3 * sizeof(unsigned long));

arch/powerpc/kernel/ptrace/ptrace-view.c

415

return membuf_write(&to, &target->thread.siar, 5 * sizeof(unsigned long));

arch/powerpc/kernel/ptrace/ptrace-vsx.c

111

return membuf_write(&to, buf, 32 * sizeof(double));

arch/powerpc/kernel/ptrace/ptrace-vsx.c

33

return membuf_write(&to, buf, 33 * sizeof(u64));

arch/riscv/kernel/ptrace.c

125

membuf_write(&to, &ptrace_vstate, sizeof(struct __riscv_v_regset_state));

arch/riscv/kernel/ptrace.c

128

return membuf_write(&to, vstate->datap, riscv_v_vsize);

arch/riscv/kernel/ptrace.c

275

return membuf_write(&to, &ctrl, sizeof(ctrl));

arch/riscv/kernel/ptrace.c

321

return membuf_write(&to, &user_cfi, sizeof(user_cfi));

arch/riscv/kernel/ptrace.c

44

return membuf_write(&to, task_pt_regs(target),

arch/riscv/kernel/ptrace.c

567

return membuf_write(&to, &cregs,

arch/riscv/kernel/ptrace.c

69

membuf_write(&to, fstate, offsetof(struct __riscv_d_ext_state, fcsr));

arch/s390/kernel/ptrace.c

570

return membuf_write(&to, &fp_regs, sizeof(fp_regs));

arch/s390/kernel/ptrace.c

629

return membuf_write(&to, target->thread.trap_tdb.data, size);

arch/s390/kernel/ptrace.c

653

return membuf_write(&to, vxrs, sizeof(vxrs));

arch/s390/kernel/ptrace.c

688

return membuf_write(&to, target->thread.ufpu.vxrs + __NUM_VXRS_LOW,

arch/s390/kernel/ptrace.c

738

return membuf_write(&to, data, sizeof(struct gs_cb));

arch/s390/kernel/ptrace.c

790

return membuf_write(&to, data, sizeof(struct gs_cb));

arch/s390/kernel/ptrace.c

849

return membuf_write(&to, data, sizeof(struct runtime_instr_cb));

arch/sh/kernel/ptrace_32.c

140

return membuf_write(&to, regs, sizeof(struct pt_regs));

arch/sh/kernel/ptrace_32.c

177

return membuf_write(&to, target->thread.xstate,

arch/sh/kernel/ptrace_32.c

217

return membuf_write(&to, regs, sizeof(struct pt_dspregs));

arch/sparc/kernel/ptrace_32.c

175

membuf_write(&to, target->thread.float_regs, 32 * sizeof(u32));

arch/sparc/kernel/ptrace_32.c

177

membuf_write(&to, &target->thread.fsr, sizeof(u32));

arch/sparc/kernel/ptrace_32.c

257

return membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u32));

arch/sparc/kernel/ptrace_32.c

295

membuf_write(&to, &target->thread.float_regs, 32 * sizeof(u32));

arch/sparc/kernel/ptrace_32.c

296

membuf_write(&to, &target->thread.fsr, sizeof(u32));

arch/sparc/kernel/ptrace_32.c

93

membuf_write(&to, regs->u_regs, 16 * sizeof(u32));

arch/sparc/kernel/ptrace_32.c

98

membuf_write(&to, uregs, 16 * sizeof(u32));

arch/sparc/kernel/ptrace_64.c

256

membuf_write(&to, regs->u_regs, 16 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

261

membuf_write(&to, &window, 16 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

263

membuf_write(&to, &regs->tstate, 3 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

354

membuf_write(&to, t->fpregs, 16 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

359

membuf_write(&to, t->fpregs + 16, 16 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

451

membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

453

membuf_write(&to, &regs->tstate, 3 * sizeof(u64));

arch/sparc/kernel/ptrace_64.c

550

membuf_write(&to, uregs, 16 * sizeof(u32));

arch/sparc/kernel/ptrace_64.c

688

membuf_write(&to, t->fpregs, 32 * sizeof(u32));

arch/sparc/kernel/ptrace_64.c

838

membuf_write(&to, t->fpregs, 32 * sizeof(u32));

arch/x86/kernel/fpu/regset.c

209

return membuf_write(&to, (unsigned long *)&cetregs->user_ssp,

arch/x86/kernel/fpu/regset.c

414

return membuf_write(&to, &fpu->fpstate->regs.fsave,

arch/x86/kernel/fpu/regset.c

429

return membuf_write(&to, &env, sizeof(env));

arch/x86/kernel/fpu/regset.c

82

return membuf_write(&to, &fpu->fpstate->regs.fxsave,

arch/x86/kernel/fpu/xstate.c

1128

membuf_write(to, from_xstate ? xstate : init_xstate, size);

arch/x86/kernel/fpu/xstate.c

1200

membuf_write(&to, xstate_fx_sw_bytes, sizeof(xsave->i387.sw_reserved));

arch/x86/kernel/fpu/xstate.c

1203

membuf_write(&to, &header, sizeof(header));

arch/x86/kernel/fpu/xstate.c

1239

membuf_write(&to, &pkru, sizeof(pkru));

arch/x86/kernel/fpu/xstate.c

1241

membuf_write(&to,

arch/x86/kernel/ptrace.c

710

return membuf_write(&to, iobm->bitmap, IO_BITMAP_BYTES);

arch/x86/kernel/tls.c

262

membuf_write(&to, &v, sizeof(v));

arch/x86/math-emu/fpu_entry.c

711

membuf_write(&to, s387, offsetof(struct swregs_state, st_space));

arch/x86/math-emu/fpu_entry.c

712

membuf_write(&to, space + offset, other);

arch/x86/math-emu/fpu_entry.c

713

membuf_write(&to, space, offset);

arch/x86/um/ptrace.c

222

membuf_write(&to, fpregs, regset->size * regset->n);

arch/x86/um/ptrace.c

94

membuf_write(&to, (void *)fxsave->st_space + i * 16, 10);

arch/xtensa/kernel/ptrace.c

146

ret = membuf_write(&to, newregs, sizeof(*newregs));

arch/xtensa/kernel/ptrace.c

64

return membuf_write(&to, &newregs, sizeof(newregs));