| /linux-6.12.1/arch/arm64/kernel/ |
| D | entry-common.c | 39 static __always_inline void __enter_from_kernel_mode(struct pt_regs *regs) in __enter_from_kernel_mode()
57 static void noinstr enter_from_kernel_mode(struct pt_regs *regs) in enter_from_kernel_mode()
72 static __always_inline void __exit_to_kernel_mode(struct pt_regs *regs) in __exit_to_kernel_mode()
92 static void noinstr exit_to_kernel_mode(struct pt_regs *regs) in exit_to_kernel_mode()
112 static __always_inline void enter_from_user_mode(struct pt_regs *regs) in enter_from_user_mode()
130 static void do_notify_resume(struct pt_regs *regs, unsigned long thread_flags) in do_notify_resume()
161 static __always_inline void exit_to_user_mode_prepare(struct pt_regs *regs) in exit_to_user_mode_prepare()
176 static __always_inline void exit_to_user_mode(struct pt_regs *regs) in exit_to_user_mode()
183 asmlinkage void noinstr asm_exit_to_user_mode(struct pt_regs *regs) in asm_exit_to_user_mode()
193 static void noinstr arm64_enter_nmi(struct pt_regs *regs) in arm64_enter_nmi()
[all …]
|
| D | traps.c | 152 static void dump_kernel_instr(const char *lvl, struct pt_regs *regs) in dump_kernel_instr()
185 static int __die(const char *str, long err, struct pt_regs *regs) in __die()
211 void die(const char *str, struct pt_regs *regs, long err) in die()
248 struct pt_regs *regs = task_pt_regs(tsk); in arm64_show_signal() local
296 void arm64_notify_die(const char *str, struct pt_regs *regs, in arm64_notify_die()
317 static u32 compat_get_it_state(struct pt_regs *regs) in compat_get_it_state()
327 static void compat_set_it_state(struct pt_regs *regs, u32 it) in compat_set_it_state()
338 static void advance_itstate(struct pt_regs *regs) in advance_itstate()
361 static void advance_itstate(struct pt_regs *regs) in advance_itstate()
366 void arm64_skip_faulting_instruction(struct pt_regs *regs, unsigned long size) in arm64_skip_faulting_instruction()
[all …]
|
| /linux-6.12.1/drivers/media/platform/samsung/s5p-jpeg/ |
| D | jpeg-hw-s5p.c | 17 void s5p_jpeg_reset(void __iomem *regs) in s5p_jpeg_reset()
30 void s5p_jpeg_poweron(void __iomem *regs) in s5p_jpeg_poweron()
35 void s5p_jpeg_input_raw_mode(void __iomem *regs, unsigned long mode) in s5p_jpeg_input_raw_mode()
51 void s5p_jpeg_proc_mode(void __iomem *regs, unsigned long mode) in s5p_jpeg_proc_mode()
65 void s5p_jpeg_subsampling_mode(void __iomem *regs, unsigned int mode) in s5p_jpeg_subsampling_mode()
80 unsigned int s5p_jpeg_get_subsampling_mode(void __iomem *regs) in s5p_jpeg_get_subsampling_mode()
85 void s5p_jpeg_dri(void __iomem *regs, unsigned int dri) in s5p_jpeg_dri()
100 void s5p_jpeg_qtbl(void __iomem *regs, unsigned int t, unsigned int n) in s5p_jpeg_qtbl()
110 void s5p_jpeg_htbl_ac(void __iomem *regs, unsigned int t) in s5p_jpeg_htbl_ac()
121 void s5p_jpeg_htbl_dc(void __iomem *regs, unsigned int t) in s5p_jpeg_htbl_dc()
[all …]
|
| D | jpeg-hw-exynos3250.c | 18 void exynos3250_jpeg_reset(void __iomem *regs) in exynos3250_jpeg_reset()
44 void exynos3250_jpeg_poweron(void __iomem *regs) in exynos3250_jpeg_poweron()
49 void exynos3250_jpeg_set_dma_num(void __iomem *regs) in exynos3250_jpeg_set_dma_num()
69 void exynos3250_jpeg_input_raw_fmt(void __iomem *regs, unsigned int fmt) in exynos3250_jpeg_input_raw_fmt()
120 void exynos3250_jpeg_set_y16(void __iomem *regs, bool y16) in exynos3250_jpeg_set_y16()
132 void exynos3250_jpeg_proc_mode(void __iomem *regs, unsigned int mode) in exynos3250_jpeg_proc_mode()
146 void exynos3250_jpeg_subsampling_mode(void __iomem *regs, unsigned int mode) in exynos3250_jpeg_subsampling_mode()
168 unsigned int exynos3250_jpeg_get_subsampling_mode(void __iomem *regs) in exynos3250_jpeg_get_subsampling_mode()
174 void exynos3250_jpeg_dri(void __iomem *regs, unsigned int dri) in exynos3250_jpeg_dri()
182 void exynos3250_jpeg_qtbl(void __iomem *regs, unsigned int t, unsigned int n) in exynos3250_jpeg_qtbl()
[all …]
|
| /linux-6.12.1/arch/arm/include/asm/ |
| D | ptrace.h | 21 struct pt_regs regs; member
28 #define user_mode(regs) \ argument
32 #define thumb_mode(regs) \ argument
35 #define thumb_mode(regs) (0) argument
39 #define isa_mode(regs) \ argument
43 #define isa_mode(regs) 1 /* Thumb */ argument
46 #define processor_mode(regs) \ argument
49 #define interrupts_enabled(regs) \ argument
52 #define fast_interrupts_enabled(regs) \ argument
58 static inline int valid_user_regs(struct pt_regs *regs) in valid_user_regs()
[all …]
|
| /linux-6.12.1/kernel/entry/ |
| D | common.c | 18 static inline void syscall_enter_audit(struct pt_regs *regs, long syscall) in syscall_enter_audit()
28 long syscall_trace_enter(struct pt_regs *regs, long syscall, in syscall_trace_enter()
74 noinstr void syscall_enter_from_user_mode_prepare(struct pt_regs *regs) in syscall_enter_from_user_mode_prepare()
83 void __weak arch_do_signal_or_restart(struct pt_regs *regs) { } in arch_do_signal_or_restart()
90 __always_inline unsigned long exit_to_user_mode_loop(struct pt_regs *regs, in exit_to_user_mode_loop()
149 static void syscall_exit_work(struct pt_regs *regs, unsigned long work) in syscall_exit_work()
180 static void syscall_exit_to_user_mode_prepare(struct pt_regs *regs) in syscall_exit_to_user_mode_prepare()
203 static __always_inline void __syscall_exit_to_user_mode_work(struct pt_regs *regs) in __syscall_exit_to_user_mode_work()
210 void syscall_exit_to_user_mode_work(struct pt_regs *regs) in syscall_exit_to_user_mode_work()
215 __visible noinstr void syscall_exit_to_user_mode(struct pt_regs *regs) in syscall_exit_to_user_mode()
[all …]
|
| /linux-6.12.1/arch/csky/include/asm/ |
| D | ptrace.h | 21 #define user_stack_pointer(regs) ((regs)->usp) argument
23 #define user_mode(regs) (!((regs)->sr & PS_S)) argument
24 #define instruction_pointer(regs) ((regs)->pc) argument
25 #define profile_pc(regs) instruction_pointer(regs) argument
26 #define trap_no(regs) ((regs->sr >> 16) & 0xff) argument
28 static inline void instruction_pointer_set(struct pt_regs *regs, in instruction_pointer_set()
40 static inline bool in_syscall(struct pt_regs const *regs) in in_syscall()
45 static inline void forget_syscall(struct pt_regs *regs) in forget_syscall()
50 static inline unsigned long regs_return_value(struct pt_regs *regs) in regs_return_value()
55 static inline void regs_set_return_value(struct pt_regs *regs, in regs_set_return_value()
[all …]
|
| /linux-6.12.1/arch/csky/kernel/probes/ |
| D | simulate-insn.c | 10 static inline bool csky_insn_reg_get_val(struct pt_regs *regs, in csky_insn_reg_get_val()
39 static inline bool csky_insn_reg_set_val(struct pt_regs *regs, in csky_insn_reg_set_val()
69 simulate_br16(u32 opcode, long addr, struct pt_regs *regs) in simulate_br16()
76 simulate_br32(u32 opcode, long addr, struct pt_regs *regs) in simulate_br32()
83 simulate_bt16(u32 opcode, long addr, struct pt_regs *regs) in simulate_bt16()
93 simulate_bt32(u32 opcode, long addr, struct pt_regs *regs) in simulate_bt32()
103 simulate_bf16(u32 opcode, long addr, struct pt_regs *regs) in simulate_bf16()
113 simulate_bf32(u32 opcode, long addr, struct pt_regs *regs) in simulate_bf32()
123 simulate_jmp16(u32 opcode, long addr, struct pt_regs *regs) in simulate_jmp16()
133 simulate_jmp32(u32 opcode, long addr, struct pt_regs *regs) in simulate_jmp32()
[all …]
|
| /linux-6.12.1/arch/loongarch/include/asm/ |
| D | ptrace.h | 20 unsigned long regs[32]; member
36 static inline int regs_irqs_disabled(struct pt_regs *regs) in regs_irqs_disabled()
41 static inline unsigned long kernel_stack_pointer(struct pt_regs *regs) in kernel_stack_pointer()
51 static inline void instruction_pointer_set(struct pt_regs *regs, unsigned long val) in instruction_pointer_set()
69 static inline unsigned long regs_get_register(struct pt_regs *regs, unsigned int offset) in regs_get_register()
85 static inline int regs_within_kernel_stack(struct pt_regs *regs, unsigned long addr) in regs_within_kernel_stack()
100 static inline unsigned long regs_get_kernel_stack_nth(struct pt_regs *regs, unsigned int n) in regs_get_kernel_stack_nth()
124 static inline unsigned long regs_get_kernel_argument(struct pt_regs *regs, in regs_get_kernel_argument()
150 #define user_mode(regs) (((regs)->csr_prmd & PLV_MASK) == PLV_USER) argument
152 static inline long regs_return_value(struct pt_regs *regs) in regs_return_value()
[all …]
|
| /linux-6.12.1/arch/mips/kernel/ |
| D | mips-r2-to-r6-emul.c | 78 static inline int mipsr6_emul(struct pt_regs *regs, u32 ir) in mipsr6_emul()
199 static int movf_func(struct pt_regs *regs, u32 ir) in movf_func()
222 static int movt_func(struct pt_regs *regs, u32 ir) in movt_func()
247 static int jr_func(struct pt_regs *regs, u32 ir) in jr_func()
304 static int movz_func(struct pt_regs *regs, u32 ir) in movz_func()
320 static int movn_func(struct pt_regs *regs, u32 ir) in movn_func()
336 static int mfhi_func(struct pt_regs *regs, u32 ir) in mfhi_func()
353 static int mthi_func(struct pt_regs *regs, u32 ir) in mthi_func()
369 static int mflo_func(struct pt_regs *regs, u32 ir) in mflo_func()
386 static int mtlo_func(struct pt_regs *regs, u32 ir) in mtlo_func()
[all …]
|
| /linux-6.12.1/arch/mips/include/asm/ |
| D | ptrace.h | 35 unsigned long regs[32]; member
54 static inline unsigned long kernel_stack_pointer(struct pt_regs *regs) in kernel_stack_pointer()
59 static inline void instruction_pointer_set(struct pt_regs *regs, in instruction_pointer_set()
79 static inline unsigned long regs_get_register(struct pt_regs *regs, in regs_get_register()
96 static inline int regs_within_kernel_stack(struct pt_regs *regs, in regs_within_kernel_stack()
112 static inline unsigned long regs_get_kernel_stack_nth(struct pt_regs *regs, in regs_get_kernel_stack_nth()
142 #define user_mode(regs) (((regs)->cp0_status & KU_MASK) == KU_USER) argument
144 static inline int is_syscall_success(struct pt_regs *regs) in is_syscall_success()
149 static inline long regs_return_value(struct pt_regs *regs) in regs_return_value()
157 #define instruction_pointer(regs) ((regs)->cp0_epc) argument
[all …]
|
| /linux-6.12.1/arch/sparc/include/asm/ |
| D | ptrace.h | 14 static inline int pt_regs_trap_type(struct pt_regs *regs) in pt_regs_trap_type()
19 static inline bool pt_regs_is_syscall(struct pt_regs *regs) in pt_regs_is_syscall()
24 static inline bool pt_regs_clear_syscall(struct pt_regs *regs) in pt_regs_clear_syscall()
64 #define user_mode(regs) (!((regs)->tstate & TSTATE_PRIV)) argument
65 #define instruction_pointer(regs) ((regs)->tpc) argument
66 #define instruction_pointer_set(regs, val) do { \ argument
70 #define user_stack_pointer(regs) ((regs)->u_regs[UREG_FP]) argument
71 static inline int is_syscall_success(struct pt_regs *regs) in is_syscall_success()
76 static inline long regs_return_value(struct pt_regs *regs) in regs_return_value()
83 #define profile_pc(regs) instruction_pointer(regs) argument
[all …]
|
| D | syscall.h | 21 struct pt_regs *regs) in syscall_get_nr()
29 struct pt_regs *regs) in syscall_rollback()
41 static inline bool syscall_has_error(struct pt_regs *regs) in syscall_has_error()
45 static inline void syscall_set_error(struct pt_regs *regs) in syscall_set_error()
49 static inline void syscall_clear_error(struct pt_regs *regs) in syscall_clear_error()
54 static inline bool syscall_has_error(struct pt_regs *regs) in syscall_has_error()
58 static inline void syscall_set_error(struct pt_regs *regs) in syscall_set_error()
62 static inline void syscall_clear_error(struct pt_regs *regs) in syscall_clear_error()
69 struct pt_regs *regs) in syscall_get_error()
77 struct pt_regs *regs) in syscall_get_return_value()
[all …]
|
| /linux-6.12.1/arch/powerpc/include/asm/ |
| D | ptrace.h | 174 #define profile_pc(regs) instruction_pointer(regs) argument
188 static inline void regs_set_return_ip(struct pt_regs *regs, unsigned long ip) in regs_set_return_ip()
194 static inline void regs_set_return_msr(struct pt_regs *regs, unsigned long msr) in regs_set_return_msr()
200 static inline void regs_add_return_ip(struct pt_regs *regs, long offset) in regs_add_return_ip()
205 static inline unsigned long instruction_pointer(struct pt_regs *regs) in instruction_pointer()
210 static inline void instruction_pointer_set(struct pt_regs *regs, in instruction_pointer_set()
216 static inline unsigned long user_stack_pointer(struct pt_regs *regs) in user_stack_pointer()
221 static inline unsigned long frame_pointer(struct pt_regs *regs) in frame_pointer()
226 #define user_mode(regs) (((regs)->msr & MSR_PR) != 0) argument
250 #define IS_CRITICAL_EXC(regs) (((regs)->trap & 2) != 0) argument
[all …]
|
| /linux-6.12.1/arch/riscv/kernel/ |
| D | traps.c | 40 static int copy_code(struct pt_regs *regs, u16 *val, const u16 *insns) in copy_code()
54 static void dump_instr(const char *loglvl, struct pt_regs *regs) in dump_instr()
75 void die(struct pt_regs *regs, const char *str) in die()
114 void do_trap(struct pt_regs *regs, int signo, int code, unsigned long addr) in do_trap()
131 static void do_trap_error(struct pt_regs *regs, int signo, int code, in do_trap_error()
170 asmlinkage __visible __trap_section void do_trap_insn_illegal(struct pt_regs *regs) in do_trap_insn_illegal()
201 asmlinkage __visible __trap_section void do_trap_load_misaligned(struct pt_regs *regs) in do_trap_load_misaligned()
222 asmlinkage __visible __trap_section void do_trap_store_misaligned(struct pt_regs *regs) in do_trap_store_misaligned()
259 static bool probe_single_step_handler(struct pt_regs *regs) in probe_single_step_handler()
266 static bool probe_breakpoint_handler(struct pt_regs *regs) in probe_breakpoint_handler()
[all …]
|
| /linux-6.12.1/arch/s390/kernel/ |
| D | traps.c | 36 static inline void __user *get_trap_ip(struct pt_regs *regs) in get_trap_ip()
54 void do_report_trap(struct pt_regs *regs, int si_signo, int si_code, char *str) in do_report_trap()
65 static void do_trap(struct pt_regs *regs, int si_signo, int si_code, char *str) in do_trap()
74 void do_per_trap(struct pt_regs *regs) in do_per_trap()
85 static void default_trap_handler(struct pt_regs *regs) in default_trap_handler()
127 static inline void do_fp_trap(struct pt_regs *regs, __u32 fpc) in do_fp_trap()
147 static void translation_specification_exception(struct pt_regs *regs) in translation_specification_exception()
153 static void illegal_op(struct pt_regs *regs) in illegal_op()
195 static void vector_exception(struct pt_regs *regs) in vector_exception()
229 static void data_exception(struct pt_regs *regs) in data_exception()
[all …]
|
| /linux-6.12.1/arch/arm64/kernel/probes/ |
| D | simulate-insn.c | 32 static inline void set_x_reg(struct pt_regs *regs, int reg, u64 val) in set_x_reg()
37 static inline void set_w_reg(struct pt_regs *regs, int reg, u64 val) in set_w_reg()
42 static inline u64 get_x_reg(struct pt_regs *regs, int reg) in get_x_reg()
47 static inline u32 get_w_reg(struct pt_regs *regs, int reg) in get_w_reg()
52 static bool __kprobes check_cbz(u32 opcode, struct pt_regs *regs) in check_cbz()
60 static bool __kprobes check_cbnz(u32 opcode, struct pt_regs *regs) in check_cbnz()
68 static bool __kprobes check_tbz(u32 opcode, struct pt_regs *regs) in check_tbz()
76 static bool __kprobes check_tbnz(u32 opcode, struct pt_regs *regs) in check_tbnz()
88 simulate_adr_adrp(u32 opcode, long addr, struct pt_regs *regs) in simulate_adr_adrp()
106 simulate_b_bl(u32 opcode, long addr, struct pt_regs *regs) in simulate_b_bl()
[all …]
|
| /linux-6.12.1/arch/s390/mm/ |
| D | fault.c | 68 static enum fault_type get_fault_type(struct pt_regs *regs) in get_fault_type()
92 static unsigned long get_fault_address(struct pt_regs *regs) in get_fault_address()
99 static __always_inline bool fault_is_write(struct pt_regs *regs) in fault_is_write()
161 static void dump_fault_info(struct pt_regs *regs) in dump_fault_info()
206 void report_user_fault(struct pt_regs *regs, long signr, int is_mm_fault) in report_user_fault()
225 static void do_sigsegv(struct pt_regs *regs, int si_code) in do_sigsegv()
231 static void handle_fault_error_nolock(struct pt_regs *regs, int si_code) in handle_fault_error_nolock()
259 static void handle_fault_error(struct pt_regs *regs, int si_code) in handle_fault_error()
267 static void do_sigbus(struct pt_regs *regs) in do_sigbus()
283 static void do_exception(struct pt_regs *regs, int access) in do_exception()
[all …]
|
| /linux-6.12.1/arch/powerpc/kernel/ |
| D | traps.c | 181 static unsigned long oops_begin(struct pt_regs *regs) in oops_begin()
207 static void oops_end(unsigned long flags, struct pt_regs *regs, in oops_end()
262 static int __die(const char *str, struct pt_regs *regs, long err) in __die()
286 void die(const char *str, struct pt_regs *regs, long err) in die()
305 void user_single_step_report(struct pt_regs *regs) in user_single_step_report()
310 static void show_signal_msg(int signr, struct pt_regs *regs, int code, in show_signal_msg()
336 static bool exception_common(int signr, struct pt_regs *regs, int code, in exception_common()
360 void _exception_pkey(struct pt_regs *regs, unsigned long addr, int key) in _exception_pkey()
368 void _exception(int signr, struct pt_regs *regs, int code, unsigned long addr) in _exception()
397 noinstr void hv_nmi_check_nonrecoverable(struct pt_regs *regs) in hv_nmi_check_nonrecoverable()
[all …]
|
| /linux-6.12.1/arch/riscv/include/asm/ |
| D | vector.h | 43 static inline void __riscv_v_vstate_clean(struct pt_regs *regs) in __riscv_v_vstate_clean()
48 static inline void __riscv_v_vstate_dirty(struct pt_regs *regs) in __riscv_v_vstate_dirty()
53 static inline void riscv_v_vstate_off(struct pt_regs *regs) in riscv_v_vstate_off()
58 static inline void riscv_v_vstate_on(struct pt_regs *regs) in riscv_v_vstate_on()
63 static inline bool riscv_v_vstate_query(struct pt_regs *regs) in riscv_v_vstate_query()
168 static inline void riscv_v_vstate_discard(struct pt_regs *regs) in riscv_v_vstate_discard()
178 struct pt_regs *regs) in riscv_v_vstate_save()
187 struct pt_regs *regs) in riscv_v_vstate_restore()
196 struct pt_regs *regs) in riscv_v_vstate_set_restore()
243 struct pt_regs *regs; in __switch_to_vector() local
[all …]
|
| /linux-6.12.1/arch/hexagon/kernel/ |
| D | traps.c | 139 struct pt_regs *regs = (struct pt_regs *) (((void *)fp) in do_show_stack() local
180 int die(const char *str, struct pt_regs *regs, long err) in die()
221 int die_if_kernel(char *str, struct pt_regs *regs, long err) in die_if_kernel()
232 static void misaligned_instruction(struct pt_regs *regs) in misaligned_instruction()
243 static void misaligned_data_load(struct pt_regs *regs) in misaligned_data_load()
249 static void misaligned_data_store(struct pt_regs *regs) in misaligned_data_store()
255 static void illegal_instruction(struct pt_regs *regs) in illegal_instruction()
265 static void precise_bus_error(struct pt_regs *regs) in precise_bus_error()
276 static void cache_error(struct pt_regs *regs) in cache_error()
285 void do_genex(struct pt_regs *regs) in do_genex()
[all …]
|
| /linux-6.12.1/arch/arm/probes/kprobes/ |
| D | actions-thumb.c | 25 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_simulate_table_branch()
45 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_simulate_mrs()
54 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_simulate_cond_branch()
79 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_simulate_branch()
107 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_simulate_ldr_literal()
159 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_emulate_ldrdstrd()
186 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_emulate_ldrstr()
212 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_emulate_rd8rn16rm0_rwflags()
239 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_emulate_rd8pc16_noflags()
259 struct arch_probes_insn *asi, struct pt_regs *regs) in t32_emulate_rd8rn16_noflags()
[all …]
|
| /linux-6.12.1/arch/sh/include/asm/ |
| D | fpu.h | 12 static inline void release_fpu(struct pt_regs *regs) in release_fpu()
17 static inline void grab_fpu(struct pt_regs *regs) in grab_fpu()
29 #define release_fpu(regs) do { } while (0) argument
30 #define grab_fpu(regs) do { } while (0) argument
31 #define fpu_state_restore(regs) do { } while (0) argument
32 #define __fpu_state_restore(regs) do { } while (0) argument
40 static inline void __unlazy_fpu(struct task_struct *tsk, struct pt_regs *regs) in __unlazy_fpu()
50 static inline void unlazy_fpu(struct task_struct *tsk, struct pt_regs *regs) in unlazy_fpu()
57 static inline void clear_fpu(struct task_struct *tsk, struct pt_regs *regs) in clear_fpu()
|
| /linux-6.12.1/arch/x86/lib/ |
| D | insn-eval.c | 179 static int resolve_default_seg(struct insn *insn, struct pt_regs *regs, int off) in resolve_default_seg()
281 static int resolve_seg_reg(struct insn *insn, struct pt_regs *regs, int regoff) in resolve_seg_reg()
343 static short get_segment_selector(struct pt_regs *regs, int seg_reg_idx) in get_segment_selector()
440 int pt_regs_offset(struct pt_regs *regs, int regno) in pt_regs_offset()
522 static int get_reg_offset(struct insn *insn, struct pt_regs *regs, in get_reg_offset()
550 static int get_reg_offset_16(struct insn *insn, struct pt_regs *regs, in get_reg_offset_16()
681 unsigned long insn_get_seg_base(struct pt_regs *regs, int seg_reg_idx) in insn_get_seg_base()
748 static unsigned long get_seg_limit(struct pt_regs *regs, int seg_reg_idx) in get_seg_limit()
796 int insn_get_code_seg_params(struct pt_regs *regs) in insn_get_code_seg_params()
855 int insn_get_modrm_rm_off(struct insn *insn, struct pt_regs *regs) in insn_get_modrm_rm_off()
[all …]
|
| /linux-6.12.1/arch/arm64/include/asm/ |
| D | ptrace.h | 159 u64 regs[31]; member
183 static inline bool in_syscall(struct pt_regs const *regs) in in_syscall()
188 static inline void forget_syscall(struct pt_regs *regs) in forget_syscall()
198 #define compat_thumb_mode(regs) \ argument
201 #define compat_thumb_mode(regs) (0) argument
204 #define user_mode(regs) \ argument
207 #define compat_user_mode(regs) \ argument
211 #define processor_mode(regs) \ argument
214 #define irqs_priority_unmasked(regs) \ argument
219 #define interrupts_enabled(regs) \ argument
[all …]
|