Searched refs:membuf_write (Results 1 - 25 of 29) sorted by relevance

12

/linux-master/arch/powerpc/kernel/ptrace/
H A Dptrace-novsx.c30 return membuf_write(&to, &target->thread.fp_state, 33 * sizeof(u64));
32 return membuf_write(&to, &empty_zero_page, 33 * sizeof(u64));
H A Dptrace-altivec.c56 membuf_write(&to, &target->thread.vr_state, 33 * sizeof(vector128));
62 return membuf_write(&to, &vrsave, sizeof(vrsave));
H A Dptrace-spe.c30 membuf_write(&to, &target->thread.evr, sizeof(target->thread.evr));
35 return membuf_write(&to, &target->thread.acc,
H A Dptrace-vsx.c33 return membuf_write(&to, buf, 33 * sizeof(u64));
111 return membuf_write(&to, buf, 32 * sizeof(double));
H A Dptrace-tm.c104 membuf_write(&to, &target->thread.ckpt_regs, sizeof(struct user_pt_regs));
249 return membuf_write(&to, buf, sizeof(buf));
362 membuf_write(&to, &target->thread.ckvr_state, 33 * sizeof(vector128));
368 return membuf_write(&to, &vrsave, sizeof(vrsave));
489 return membuf_write(&to, buf, 32 * sizeof(double));
591 membuf_write(&to, &target->thread.tm_tfhar, sizeof(u64));
593 membuf_write(&to, &target->thread.tm_texasr, sizeof(u64));
595 return membuf_write(&to, &target->thread.tm_tfiar, sizeof(u64));
673 return membuf_write(&to, &target->thread.tm_tar, sizeof(u64));
714 return membuf_write(
[all...]
H A Dptrace-view.c228 membuf_write(&to, target->thread.regs, sizeof(struct user_pt_regs));
296 return membuf_write(&to, &target->thread.regs->ppr, sizeof(u64));
313 return membuf_write(&to, &target->thread.dscr, sizeof(u64));
327 return membuf_write(&to, &target->thread.tar, sizeof(u64));
361 return membuf_write(&to, &target->thread.ebbrr, 3 * sizeof(unsigned long));
415 return membuf_write(&to, &target->thread.siar, 5 * sizeof(unsigned long));
/linux-master/arch/nios2/kernel/
H A Dptrace.c29 membuf_write(&to, &regs->r1, 7 * 4); // R1..R7
30 membuf_write(&to, &regs->r8, 8 * 4); // R8..R15
31 membuf_write(&to, sw, 8 * 4); // R16..R23
/linux-master/arch/loongarch/kernel/
H A Dptrace.c82 r = membuf_write(&to, &regs->regs, sizeof(u64) * GPR_NUM);
83 r = membuf_write(&to, &regs->orig_a0, sizeof(u64));
84 r = membuf_write(&to, &regs->csr_era, sizeof(u64));
85 r = membuf_write(&to, &regs->csr_badvaddr, sizeof(u64));
123 return membuf_write(to, &target->thread.fpu.fpr,
135 r = membuf_write(to, &fpr_val, sizeof(elf_fpreg_t));
158 r = membuf_write(&to, &target->thread.fpu.fcc, sizeof(target->thread.fpu.fcc));
159 r = membuf_write(&to, &target->thread.fpu.fcsr, sizeof(target->thread.fpu.fcsr));
239 r = membuf_write(&to, &cfg_val, sizeof(u32));
271 membuf_write(t
[all...]
/linux-master/arch/sparc/kernel/
H A Dptrace_32.c93 membuf_write(&to, regs->u_regs, 16 * sizeof(u32));
98 membuf_write(&to, uregs, 16 * sizeof(u32));
175 membuf_write(&to, target->thread.float_regs, 32 * sizeof(u32));
177 membuf_write(&to, &target->thread.fsr, sizeof(u32));
257 return membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u32));
295 membuf_write(&to, &target->thread.float_regs, 32 * sizeof(u32));
296 membuf_write(&to, &target->thread.fsr, sizeof(u32));
H A Dptrace_64.c256 membuf_write(&to, regs->u_regs, 16 * sizeof(u64));
261 membuf_write(&to, &window, 16 * sizeof(u64));
263 membuf_write(&to, &regs->tstate, 3 * sizeof(u64));
354 membuf_write(&to, t->fpregs, 16 * sizeof(u64));
359 membuf_write(&to, t->fpregs + 16, 16 * sizeof(u64));
451 membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u64));
453 membuf_write(&to, &regs->tstate, 3 * sizeof(u64));
550 membuf_write(&to, uregs, 16 * sizeof(u32));
688 membuf_write(&to, t->fpregs, 32 * sizeof(u32));
838 membuf_write(
[all...]
/linux-master/arch/riscv/kernel/
H A Dptrace.c37 return membuf_write(&to, task_pt_regs(target),
62 membuf_write(&to, fstate, offsetof(struct __riscv_d_ext_state, fcsr));
115 membuf_write(&to, &ptrace_vstate, sizeof(struct __riscv_v_regset_state));
118 return membuf_write(&to, vstate->datap, riscv_v_vsize);
320 return membuf_write(&to, &cregs,
/linux-master/arch/x86/kernel/fpu/
H A Dregset.c82 return membuf_write(&to, &fpu->fpstate->regs.fxsave,
208 return membuf_write(&to, (unsigned long *)&cetregs->user_ssp,
413 return membuf_write(&to, &fpu->fpstate->regs.fsave,
428 return membuf_write(&to, &env, sizeof(env));
H A Dxstate.c1046 membuf_write(to, from_xstate ? xstate : init_xstate, size);
1119 membuf_write(&to, xstate_fx_sw_bytes, sizeof(xsave->i387.sw_reserved));
1122 membuf_write(&to, &header, sizeof(header));
1157 membuf_write(&to, &pkru, sizeof(pkru));
1159 membuf_write(&to,
/linux-master/arch/arm64/kernel/
H A Dptrace.c487 membuf_write(&to, &info, sizeof(info));
559 return membuf_write(&to, uregs, sizeof(*uregs));
600 return membuf_write(&to, uregs, sizeof(*uregs));
824 membuf_write(&to, &header, sizeof(header));
839 membuf_write(&to, target->thread.sve_state, end - start);
851 membuf_write(&to, &target->thread.uw.fpsimd_state.fpsr,
1076 membuf_write(&to, &header, sizeof(header));
1088 membuf_write(&to, target->thread.sme_state, end - start);
1194 membuf_write(&to, thread_zt_state(&target->thread),
1257 return membuf_write(
[all...]
/linux-master/arch/mips/kernel/
H A Dptrace.c225 return membuf_write(&to, uregs, sizeof(uregs));
290 return membuf_write(&to, uregs, sizeof(uregs));
416 membuf_write(to, &target->thread.fpu,
449 membuf_write(&to, &target->thread.fpu.fcr31, sizeof(u32));
450 membuf_write(&to, &boot_cpu_data.fpu_id, sizeof(u32));
616 membuf_write(to, &target->thread.fpu.fpr[i], cp_sz);
642 membuf_write(&to, &target->thread.fpu.fpr, wr_size);
649 return membuf_write(&to, &ctrl_regs, sizeof(ctrl_regs));
715 return membuf_write(&to, dspregs, sizeof(dspregs));
781 return membuf_write(
[all...]
/linux-master/arch/csky/kernel/
H A Dptrace.c86 return membuf_write(&to, regs, sizeof(*regs));
131 return membuf_write(&to, &tmp, sizeof(tmp));
133 return membuf_write(&to, regs, sizeof(*regs));
/linux-master/arch/sh/kernel/
H A Dptrace_32.c140 return membuf_write(&to, regs, sizeof(struct pt_regs));
177 return membuf_write(&to, target->thread.xstate,
217 return membuf_write(&to, regs, sizeof(struct pt_dspregs));
/linux-master/include/linux/
H A Dregset.h37 static inline int membuf_write(struct membuf *s, const void *v, size_t size) function
/linux-master/arch/openrisc/kernel/
H A Dptrace.c56 membuf_write(&to, regs->gpr + 1, 31 * 4);
/linux-master/arch/hexagon/kernel/
H A Dptrace.c48 membuf_write(&to, &regs->r00, 32*sizeof(unsigned long));
/linux-master/arch/x86/math-emu/
H A Dfpu_entry.c711 membuf_write(&to, s387, offsetof(struct swregs_state, st_space));
712 membuf_write(&to, space + offset, other);
713 membuf_write(&to, space, offset);
/linux-master/arch/arm/kernel/
H A Dptrace.c548 return membuf_write(&to, task_pt_regs(target), sizeof(struct pt_regs));
576 return membuf_write(&to, &task_thread_info(target)->fpstate,
621 membuf_write(&to, vfp->fpregs, sizeof(vfp->fpregs));
/linux-master/arch/arc/kernel/
H A Dptrace.c252 return membuf_write(&to, &regs->r30, sizeof(struct user_regs_arcv2));
255 membuf_write(&to, &regs->r30, 4); /* r30 only */
/linux-master/arch/x86/kernel/
H A Dtls.c262 membuf_write(&to, &v, sizeof(v));
/linux-master/arch/m68k/kernel/
H A Dptrace.c310 return membuf_write(&to, uregs, sizeof(uregs));

Completed in 185 milliseconds

12