Home
last modified time | relevance | path

Searched refs:membuf_write (Results 1 – 25 of 30) sorted by relevance

12

/openbmc/linux/arch/loongarch/kernel/
H A Dptrace.c82 r = membuf_write(&to, &regs->regs, sizeof(u64) * GPR_NUM); in gpr_get()
83 r = membuf_write(&to, &regs->orig_a0, sizeof(u64)); in gpr_get()
84 r = membuf_write(&to, &regs->csr_era, sizeof(u64)); in gpr_get()
85 r = membuf_write(&to, &regs->csr_badvaddr, sizeof(u64)); in gpr_get()
123 return membuf_write(to, &target->thread.fpu.fpr, in gfpr_get()
135 r = membuf_write(to, &fpr_val, sizeof(elf_fpreg_t)); in gfpr_get_simd()
239 r = membuf_write(&to, &cfg_val, sizeof(u32)); in cfg_get()
271 membuf_write(to, &target->thread.fpu.fpr[i], cp_sz); in copy_pad_fprs()
299 membuf_write(&to, &target->thread.fpu.fpr, wr_size); in simd_get()
354 r = membuf_write(&to, &target->thread.fpu.ftop, sizeof(u32)); in lbt_get()
[all …]
/openbmc/linux/arch/powerpc/kernel/ptrace/
H A Dptrace-tm.c104 membuf_write(&to, &target->thread.ckpt_regs, sizeof(struct user_pt_regs)); in tm_cgpr_get()
249 return membuf_write(&to, buf, sizeof(buf)); in tm_cfpr_get()
362 membuf_write(&to, &target->thread.ckvr_state, 33 * sizeof(vector128)); in tm_cvmx_get()
368 return membuf_write(&to, &vrsave, sizeof(vrsave)); in tm_cvmx_get()
489 return membuf_write(&to, buf, 32 * sizeof(double)); in tm_cvsx_get()
591 membuf_write(&to, &target->thread.tm_tfhar, sizeof(u64)); in tm_spr_get()
593 membuf_write(&to, &target->thread.tm_texasr, sizeof(u64)); in tm_spr_get()
595 return membuf_write(&to, &target->thread.tm_tfiar, sizeof(u64)); in tm_spr_get()
673 return membuf_write(&to, &target->thread.tm_tar, sizeof(u64)); in tm_tar_get()
714 return membuf_write(&to, &target->thread.tm_ppr, sizeof(u64)); in tm_ppr_get()
[all …]
H A Dptrace-novsx.c30 return membuf_write(&to, &target->thread.fp_state, 33 * sizeof(u64)); in fpr_get()
32 return membuf_write(&to, &empty_zero_page, 33 * sizeof(u64)); in fpr_get()
H A Dptrace-spe.c30 membuf_write(&to, &target->thread.evr, sizeof(target->thread.evr)); in evr_get()
35 return membuf_write(&to, &target->thread.acc, in evr_get()
H A Dptrace-altivec.c56 membuf_write(&to, &target->thread.vr_state, 33 * sizeof(vector128)); in vr_get()
62 return membuf_write(&to, &vrsave, sizeof(vrsave)); in vr_get()
H A Dptrace-vsx.c33 return membuf_write(&to, buf, 33 * sizeof(u64)); in fpr_get()
111 return membuf_write(&to, buf, 32 * sizeof(double)); in vsr_get()
H A Dptrace-view.c228 membuf_write(&to, target->thread.regs, sizeof(struct user_pt_regs)); in gpr_get()
296 return membuf_write(&to, &target->thread.regs->ppr, sizeof(u64)); in ppr_get()
313 return membuf_write(&to, &target->thread.dscr, sizeof(u64)); in dscr_get()
327 return membuf_write(&to, &target->thread.tar, sizeof(u64)); in tar_get()
361 return membuf_write(&to, &target->thread.ebbrr, 3 * sizeof(unsigned long)); in ebb_get()
415 return membuf_write(&to, &target->thread.siar, 5 * sizeof(unsigned long)); in pmu_get()
/openbmc/linux/arch/sparc/kernel/
H A Dptrace_32.c93 membuf_write(&to, regs->u_regs, 16 * sizeof(u32)); in genregs32_get()
98 membuf_write(&to, uregs, 16 * sizeof(u32)); in genregs32_get()
175 membuf_write(&to, target->thread.float_regs, 32 * sizeof(u32)); in fpregs32_get()
177 membuf_write(&to, &target->thread.fsr, sizeof(u32)); in fpregs32_get()
257 return membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u32)); in getregs_get()
295 membuf_write(&to, &target->thread.float_regs, 32 * sizeof(u32)); in getfpregs_get()
296 membuf_write(&to, &target->thread.fsr, sizeof(u32)); in getfpregs_get()
H A Dptrace_64.c256 membuf_write(&to, regs->u_regs, 16 * sizeof(u64)); in genregs64_get()
261 membuf_write(&to, &window, 16 * sizeof(u64)); in genregs64_get()
263 membuf_write(&to, &regs->tstate, 3 * sizeof(u64)); in genregs64_get()
354 membuf_write(&to, t->fpregs, 16 * sizeof(u64)); in fpregs64_get()
359 membuf_write(&to, t->fpregs + 16, 16 * sizeof(u64)); in fpregs64_get()
451 membuf_write(&to, regs->u_regs + 1, 15 * sizeof(u64)); in getregs64_get()
453 membuf_write(&to, &regs->tstate, 3 * sizeof(u64)); in getregs64_get()
550 membuf_write(&to, uregs, 16 * sizeof(u32)); in genregs32_get()
688 membuf_write(&to, t->fpregs, 32 * sizeof(u32)); in fpregs32_get()
838 membuf_write(&to, t->fpregs, 32 * sizeof(u32)); in getfpregs_get()
/openbmc/linux/arch/nios2/kernel/
H A Dptrace.c29 membuf_write(&to, &regs->r1, 7 * 4); // R1..R7 in genregs_get()
30 membuf_write(&to, &regs->r8, 8 * 4); // R8..R15 in genregs_get()
31 membuf_write(&to, sw, 8 * 4); // R16..R23 in genregs_get()
/openbmc/linux/arch/riscv/kernel/
H A Dptrace.c37 return membuf_write(&to, task_pt_regs(target), in riscv_gpr_get()
62 membuf_write(&to, fstate, offsetof(struct __riscv_d_ext_state, fcsr)); in riscv_fpr_get()
112 membuf_write(&to, &ptrace_vstate, sizeof(struct __riscv_v_regset_state)); in riscv_vr_get()
115 return membuf_write(&to, vstate->datap, riscv_v_vsize); in riscv_vr_get()
317 return membuf_write(&to, &cregs, in compat_riscv_gpr_get()
/openbmc/linux/arch/mips/kernel/
H A Dptrace.c225 return membuf_write(&to, uregs, sizeof(uregs)); in gpr32_get()
290 return membuf_write(&to, uregs, sizeof(uregs)); in gpr64_get()
416 membuf_write(to, &target->thread.fpu, in fpr_get_fpa()
449 membuf_write(&to, &target->thread.fpu.fcr31, sizeof(u32)); in fpr_get()
450 membuf_write(&to, &boot_cpu_data.fpu_id, sizeof(u32)); in fpr_get()
616 membuf_write(to, &target->thread.fpu.fpr[i], cp_sz); in copy_pad_fprs()
642 membuf_write(&to, &target->thread.fpu.fpr, wr_size); in msa_get()
649 return membuf_write(&to, &ctrl_regs, sizeof(ctrl_regs)); in msa_get()
715 return membuf_write(&to, dspregs, sizeof(dspregs)); in dsp32_get()
781 return membuf_write(&to, dspregs, sizeof(dspregs)); in dsp64_get()
/openbmc/linux/arch/x86/kernel/fpu/
H A Dregset.c82 return membuf_write(&to, &fpu->fpstate->regs.fxsave, in xfpregs_get()
208 return membuf_write(&to, (unsigned long *)&cetregs->user_ssp, in ssp_get()
413 return membuf_write(&to, &fpu->fpstate->regs.fsave, in fpregs_get()
428 return membuf_write(&to, &env, sizeof(env)); in fpregs_get()
H A Dxstate.c1049 membuf_write(to, from_xstate ? xstate : init_xstate, size); in copy_feature()
1122 membuf_write(&to, xstate_fx_sw_bytes, sizeof(xsave->i387.sw_reserved)); in __copy_xstate_to_uabi_buf()
1125 membuf_write(&to, &header, sizeof(header)); in __copy_xstate_to_uabi_buf()
1160 membuf_write(&to, &pkru, sizeof(pkru)); in __copy_xstate_to_uabi_buf()
1162 membuf_write(&to, in __copy_xstate_to_uabi_buf()
/openbmc/linux/arch/arm64/kernel/
H A Dptrace.c487 membuf_write(&to, &info, sizeof(info)); in hw_break_get()
559 return membuf_write(&to, uregs, sizeof(*uregs)); in gpr_get()
600 return membuf_write(&to, uregs, sizeof(*uregs)); in __fpr_get()
791 membuf_write(&to, &header, sizeof(header)); in sve_get_common()
818 membuf_write(&to, &target->thread.uw.fpsimd_state.fpsr, in sve_get_common()
1043 membuf_write(&to, &header, sizeof(header)); in za_get()
1161 membuf_write(&to, thread_zt_state(&target->thread), in zt_get()
1224 return membuf_write(&to, &uregs, sizeof(uregs)); in pac_mask_get()
1305 return membuf_write(&to, &user_keys, sizeof(user_keys)); in pac_address_keys_get()
1354 return membuf_write(&to, &user_keys, sizeof(user_keys)); in pac_generic_keys_get()
[all …]
/openbmc/linux/arch/sh/kernel/
H A Dptrace_32.c140 return membuf_write(&to, regs, sizeof(struct pt_regs)); in genregs_get()
177 return membuf_write(&to, target->thread.xstate, in fpregs_get()
217 return membuf_write(&to, regs, sizeof(struct pt_dspregs)); in dspregs_get()
/openbmc/linux/arch/csky/kernel/
H A Dptrace.c86 return membuf_write(&to, regs, sizeof(*regs)); in gpr_get()
131 return membuf_write(&to, &tmp, sizeof(tmp)); in fpr_get()
133 return membuf_write(&to, regs, sizeof(*regs)); in fpr_get()
/openbmc/linux/arch/x86/math-emu/
H A Dfpu_entry.c711 membuf_write(&to, s387, offsetof(struct swregs_state, st_space)); in fpregs_soft_get()
712 membuf_write(&to, space + offset, other); in fpregs_soft_get()
713 membuf_write(&to, space, offset); in fpregs_soft_get()
/openbmc/linux/arch/s390/kernel/
H A Dptrace.c898 return membuf_write(&to, &fp_regs, sizeof(fp_regs)); in s390_fpregs_get()
966 return membuf_write(&to, target->thread.trap_tdb.data, size); in s390_tdb_get()
990 return membuf_write(&to, vxrs, sizeof(vxrs)); in s390_vxrs_low_get()
1025 return membuf_write(&to, target->thread.fpu.vxrs + __NUM_VXRS_LOW, in s390_vxrs_high_get()
1075 return membuf_write(&to, data, sizeof(struct gs_cb)); in s390_gs_cb_get()
1127 return membuf_write(&to, data, sizeof(struct gs_cb)); in s390_gs_bc_get()
1186 return membuf_write(&to, data, sizeof(struct runtime_instr_cb)); in s390_runtime_instr_get()
/openbmc/linux/arch/openrisc/kernel/
H A Dptrace.c56 membuf_write(&to, regs->gpr + 1, 31 * 4); in genregs_get()
/openbmc/linux/arch/arm/kernel/
H A Dptrace.c548 return membuf_write(&to, task_pt_regs(target), sizeof(struct pt_regs)); in gpr_get()
576 return membuf_write(&to, &task_thread_info(target)->fpstate, in fpa_get()
621 membuf_write(&to, vfp->fpregs, sizeof(vfp->fpregs)); in vfp_get()
/openbmc/linux/arch/hexagon/kernel/
H A Dptrace.c48 membuf_write(&to, &regs->r00, 32*sizeof(unsigned long)); in genregs_get()
/openbmc/linux/include/linux/
H A Dregset.h37 static inline int membuf_write(struct membuf *s, const void *v, size_t size) in membuf_write() function
/openbmc/linux/arch/arc/kernel/
H A Dptrace.c252 return membuf_write(&to, &regs->r30, sizeof(struct user_regs_arcv2)); in arcv2regs_get()
255 membuf_write(&to, &regs->r30, 4); /* r30 only */ in arcv2regs_get()
/openbmc/linux/arch/x86/kernel/
H A Dtls.c262 membuf_write(&to, &v, sizeof(v)); in regset_tls_get()

12