Home
last modified time | relevance | path

Searched refs:regs (Results 226 - 250 of 7312) sorted by relevance

12345678910>>...293

/kernel/linux/linux-5.10/arch/sh/include/asm/
H A Delf.h102 * This covers all of general/DSP/FPU regs.
136 do { _r->regs[0]=0; _r->regs[1]=0; _r->regs[2]=0; _r->regs[3]=0; \
137 _r->regs[4]=0; _r->regs[5]=0; _r->regs[6]=0; _r->regs[7]=0; \
138 _r->regs[
[all...]
/kernel/linux/linux-5.10/arch/sparc/include/asm/
H A Dsyscall.h21 struct pt_regs *regs) in syscall_get_nr()
23 int syscall_p = pt_regs_is_syscall(regs); in syscall_get_nr()
25 return (syscall_p ? regs->u_regs[UREG_G1] : -1L); 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() argument
43 return (regs->psr & PSR_C) ? true : false; in syscall_has_error()
45 static inline void syscall_set_error(struct pt_regs *regs) in syscall_set_error() argument
47 regs->psr |= PSR_C; in syscall_set_error()
49 static inline void syscall_clear_error(struct pt_regs *regs) in syscall_clear_error() argument
51 regs in syscall_clear_error()
20 syscall_get_nr(struct task_struct *task, struct pt_regs *regs) syscall_get_nr() argument
28 syscall_rollback(struct task_struct *task, struct pt_regs *regs) syscall_rollback() argument
54 syscall_has_error(struct pt_regs *regs) syscall_has_error() argument
58 syscall_set_error(struct pt_regs *regs) syscall_set_error() argument
62 syscall_clear_error(struct pt_regs *regs) syscall_clear_error() argument
68 syscall_get_error(struct task_struct *task, struct pt_regs *regs) syscall_get_error() argument
76 syscall_get_return_value(struct task_struct *task, struct pt_regs *regs) syscall_get_return_value() argument
84 syscall_set_return_value(struct task_struct *task, struct pt_regs *regs, int error, long val) syscall_set_return_value() argument
97 syscall_get_arguments(struct task_struct *task, struct pt_regs *regs, unsigned long *args) syscall_get_arguments() argument
120 syscall_set_arguments(struct task_struct *task, struct pt_regs *regs, const unsigned long *args) syscall_set_arguments() argument
[all...]
/kernel/linux/linux-6.6/arch/microblaze/kernel/
H A Dexceptions.c54 asmlinkage void sw_exception(struct pt_regs *regs) in sw_exception() argument
56 _exception(SIGTRAP, regs, TRAP_BRKPT, regs->r16); in sw_exception()
57 flush_dcache_range(regs->r16, regs->r16 + 0x4); in sw_exception()
58 flush_icache_range(regs->r16, regs->r16 + 0x4); in sw_exception()
61 void _exception(int signr, struct pt_regs *regs, int code, unsigned long addr) in _exception() argument
63 if (kernel_mode(regs)) in _exception()
64 die("Exception in kernel mode", regs, sign in _exception()
69 full_exception(struct pt_regs *regs, unsigned int type, int fsr, int addr) full_exception() argument
[all...]
/kernel/linux/linux-6.6/arch/sh/include/asm/
H A Delf.h102 * This covers all of general/DSP/FPU regs.
136 do { _r->regs[0]=0; _r->regs[1]=0; _r->regs[2]=0; _r->regs[3]=0; \
137 _r->regs[4]=0; _r->regs[5]=0; _r->regs[6]=0; _r->regs[7]=0; \
138 _r->regs[
[all...]
/kernel/linux/linux-6.6/arch/x86/include/asm/
H A Dsyscall.h38 static inline int syscall_get_nr(struct task_struct *task, struct pt_regs *regs) in syscall_get_nr() argument
40 return regs->orig_ax; in syscall_get_nr()
44 struct pt_regs *regs) in syscall_rollback()
46 regs->ax = regs->orig_ax; in syscall_rollback()
50 struct pt_regs *regs) in syscall_get_error()
52 unsigned long error = regs->ax; in syscall_get_error()
69 struct pt_regs *regs) in syscall_get_return_value()
71 return regs->ax; in syscall_get_return_value()
75 struct pt_regs *regs, in syscall_set_return_value()
43 syscall_rollback(struct task_struct *task, struct pt_regs *regs) syscall_rollback() argument
49 syscall_get_error(struct task_struct *task, struct pt_regs *regs) syscall_get_error() argument
68 syscall_get_return_value(struct task_struct *task, struct pt_regs *regs) syscall_get_return_value() argument
74 syscall_set_return_value(struct task_struct *task, struct pt_regs *regs, int error, long val) syscall_set_return_value() argument
83 syscall_get_arguments(struct task_struct *task, struct pt_regs *regs, unsigned long *args) syscall_get_arguments() argument
97 syscall_get_arguments(struct task_struct *task, struct pt_regs *regs, unsigned long *args) syscall_get_arguments() argument
[all...]
/kernel/linux/linux-5.10/arch/mips/kernel/
H A Dkgdb.c57 { "zero", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[0]) },
58 { "at", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[1]) },
59 { "v0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[2]) },
60 { "v1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[3]) },
61 { "a0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[4]) },
62 { "a1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[5]) },
63 { "a2", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[6]) },
64 { "a3", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[7]) },
65 { "t0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[8]) },
66 { "t1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[
131 dbg_set_reg(int regno, void *mem, struct pt_regs *regs) dbg_set_reg() argument
164 dbg_get_reg(int regno, void *mem, struct pt_regs *regs) dbg_get_reg() argument
290 kgdb_arch_set_pc(struct pt_regs *regs, unsigned long pc) kgdb_arch_set_pc() argument
303 struct pt_regs *regs = args->regs; kgdb_mips_notify() local
325 kgdb_nmicallback(smp_processor_id(), regs); kgdb_mips_notify() local
345 kgdb_ll_trap(int cmd, const char *str, struct pt_regs *regs, long err, int trap, int sig) kgdb_ll_trap() argument
371 kgdb_arch_handle_exception(int vector, int signo, int err_code, char *remcom_in_buffer, char *remcom_out_buffer, struct pt_regs *regs) kgdb_arch_handle_exception() argument
[all...]
/kernel/linux/linux-6.6/arch/mips/kernel/
H A Dkgdb.c56 { "zero", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[0]) },
57 { "at", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[1]) },
58 { "v0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[2]) },
59 { "v1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[3]) },
60 { "a0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[4]) },
61 { "a1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[5]) },
62 { "a2", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[6]) },
63 { "a3", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[7]) },
64 { "t0", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[8]) },
65 { "t1", GDB_SIZEOF_REG, offsetof(struct pt_regs, regs[
130 dbg_set_reg(int regno, void *mem, struct pt_regs *regs) dbg_set_reg() argument
163 dbg_get_reg(int regno, void *mem, struct pt_regs *regs) dbg_get_reg() argument
277 kgdb_arch_set_pc(struct pt_regs *regs, unsigned long pc) kgdb_arch_set_pc() argument
290 struct pt_regs *regs = args->regs; kgdb_mips_notify() local
324 kgdb_ll_trap(int cmd, const char *str, struct pt_regs *regs, long err, int trap, int sig) kgdb_ll_trap() argument
350 kgdb_arch_handle_exception(int vector, int signo, int err_code, char *remcom_in_buffer, char *remcom_out_buffer, struct pt_regs *regs) kgdb_arch_handle_exception() argument
[all...]
/kernel/linux/linux-5.10/drivers/rtc/
H A Drtc-fm3130.c48 u8 regs[15]; member
69 fm3130->regs[FM3130_RTC_CONTROL] = in fm3130_rtc_mode()
73 fm3130->regs[FM3130_RTC_CONTROL] &= in fm3130_rtc_mode()
78 fm3130->regs[FM3130_RTC_CONTROL] |= FM3130_RTC_CONTROL_BIT_WRITE; in fm3130_rtc_mode()
81 fm3130->regs[FM3130_RTC_CONTROL] |= FM3130_RTC_CONTROL_BIT_READ; in fm3130_rtc_mode()
89 FM3130_RTC_CONTROL, fm3130->regs[FM3130_RTC_CONTROL]); in fm3130_rtc_mode()
115 dev_dbg(dev, "%s: %15ph\n", "read", fm3130->regs); in fm3130_get_time()
117 t->tm_sec = bcd2bin(fm3130->regs[FM3130_RTC_SECONDS] & 0x7f); in fm3130_get_time()
118 t->tm_min = bcd2bin(fm3130->regs[FM3130_RTC_MINUTES] & 0x7f); in fm3130_get_time()
119 tmp = fm3130->regs[FM3130_RTC_HOUR in fm3130_get_time()
[all...]
H A Drtc-mpc5121.c79 struct mpc5121_rtc_regs __iomem *regs; member
89 static void mpc5121_rtc_update_smh(struct mpc5121_rtc_regs __iomem *regs, in mpc5121_rtc_update_smh() argument
92 out_8(&regs->second_set, tm->tm_sec); in mpc5121_rtc_update_smh()
93 out_8(&regs->minute_set, tm->tm_min); in mpc5121_rtc_update_smh()
94 out_8(&regs->hour_set, tm->tm_hour); in mpc5121_rtc_update_smh()
97 out_8(&regs->set_time, 0x1); in mpc5121_rtc_update_smh()
98 out_8(&regs->set_time, 0x3); in mpc5121_rtc_update_smh()
99 out_8(&regs->set_time, 0x1); in mpc5121_rtc_update_smh()
100 out_8(&regs->set_time, 0x0); in mpc5121_rtc_update_smh()
106 struct mpc5121_rtc_regs __iomem *regs in mpc5121_rtc_read_time() local
128 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_set_time() local
150 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5200_rtc_read_time() local
177 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5200_rtc_set_time() local
199 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_read_alarm() local
211 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_set_alarm() local
243 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_handler() local
260 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_handler_upd() local
277 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_alarm_irq_enable() local
391 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_remove() local
[all...]
/kernel/linux/linux-6.6/drivers/rtc/
H A Drtc-fm3130.c48 u8 regs[15]; member
69 fm3130->regs[FM3130_RTC_CONTROL] = in fm3130_rtc_mode()
73 fm3130->regs[FM3130_RTC_CONTROL] &= in fm3130_rtc_mode()
78 fm3130->regs[FM3130_RTC_CONTROL] |= FM3130_RTC_CONTROL_BIT_WRITE; in fm3130_rtc_mode()
81 fm3130->regs[FM3130_RTC_CONTROL] |= FM3130_RTC_CONTROL_BIT_READ; in fm3130_rtc_mode()
89 FM3130_RTC_CONTROL, fm3130->regs[FM3130_RTC_CONTROL]); in fm3130_rtc_mode()
115 dev_dbg(dev, "%s: %15ph\n", "read", fm3130->regs); in fm3130_get_time()
117 t->tm_sec = bcd2bin(fm3130->regs[FM3130_RTC_SECONDS] & 0x7f); in fm3130_get_time()
118 t->tm_min = bcd2bin(fm3130->regs[FM3130_RTC_MINUTES] & 0x7f); in fm3130_get_time()
119 tmp = fm3130->regs[FM3130_RTC_HOUR in fm3130_get_time()
[all...]
H A Drtc-mpc5121.c77 struct mpc5121_rtc_regs __iomem *regs; member
87 static void mpc5121_rtc_update_smh(struct mpc5121_rtc_regs __iomem *regs, in mpc5121_rtc_update_smh() argument
90 out_8(&regs->second_set, tm->tm_sec); in mpc5121_rtc_update_smh()
91 out_8(&regs->minute_set, tm->tm_min); in mpc5121_rtc_update_smh()
92 out_8(&regs->hour_set, tm->tm_hour); in mpc5121_rtc_update_smh()
95 out_8(&regs->set_time, 0x1); in mpc5121_rtc_update_smh()
96 out_8(&regs->set_time, 0x3); in mpc5121_rtc_update_smh()
97 out_8(&regs->set_time, 0x1); in mpc5121_rtc_update_smh()
98 out_8(&regs->set_time, 0x0); in mpc5121_rtc_update_smh()
104 struct mpc5121_rtc_regs __iomem *regs in mpc5121_rtc_read_time() local
126 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_set_time() local
148 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5200_rtc_read_time() local
175 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5200_rtc_set_time() local
197 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_read_alarm() local
209 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_set_alarm() local
227 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_handler() local
244 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_handler_upd() local
261 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_alarm_irq_enable() local
376 struct mpc5121_rtc_regs __iomem *regs = rtc->regs; mpc5121_rtc_remove() local
[all...]
/kernel/linux/linux-6.6/arch/xtensa/kernel/
H A Dtraps.c52 static void do_illegal_instruction(struct pt_regs *regs);
53 static void do_div0(struct pt_regs *regs);
54 static void do_interrupt(struct pt_regs *regs);
56 static void do_nmi(struct pt_regs *regs);
59 static void do_load_store(struct pt_regs *regs);
61 static void do_unaligned_user(struct pt_regs *regs);
62 static void do_multihit(struct pt_regs *regs);
64 static void do_coprocessor(struct pt_regs *regs);
66 static void do_debug(struct pt_regs *regs);
174 __die_if_kernel(const char *str, struct pt_regs *regs, lon argument
181 dump_user_code(struct pt_regs *regs) dump_user_code() argument
192 dump_user_code(struct pt_regs *regs) dump_user_code() argument
201 do_unhandled(struct pt_regs *regs) do_unhandled() argument
220 do_multihit(struct pt_regs *regs) do_multihit() argument
261 do_nmi(struct pt_regs *regs) do_nmi() argument
274 do_interrupt(struct pt_regs *regs) do_interrupt() argument
313 do_IRQ(__ffs(int_at_level), regs); do_interrupt() local
320 check_div0(struct pt_regs *regs) check_div0() argument
342 do_illegal_instruction(struct pt_regs *regs) do_illegal_instruction() argument
370 do_div0(struct pt_regs *regs) do_div0() argument
377 do_load_store(struct pt_regs *regs) do_load_store() argument
396 do_unaligned_user(struct pt_regs *regs) do_unaligned_user() argument
409 do_coprocessor(struct pt_regs *regs) do_coprocessor() argument
421 do_debug(struct pt_regs *regs) do_debug() argument
529 show_regs(struct pt_regs * regs) show_regs() argument
629 die(const char * str, struct pt_regs * regs, long err) die() argument
[all...]
/kernel/linux/linux-6.6/arch/sparc/kernel/
H A Dunaligned_32.c94 static inline unsigned long fetch_reg(unsigned int reg, struct pt_regs *regs) in fetch_reg() argument
99 return (!reg ? 0 : regs->u_regs[reg]); in fetch_reg()
102 win = (struct reg_window32 *) regs->u_regs[UREG_FP]; in fetch_reg()
106 static inline unsigned long safe_fetch_reg(unsigned int reg, struct pt_regs *regs) in safe_fetch_reg() argument
112 return (!reg ? 0 : regs->u_regs[reg]); in safe_fetch_reg()
115 win = (struct reg_window32 __user *) regs->u_regs[UREG_FP]; in safe_fetch_reg()
126 static inline unsigned long *fetch_reg_addr(unsigned int reg, struct pt_regs *regs) in fetch_reg_addr() argument
131 return &regs->u_regs[reg]; in fetch_reg_addr()
132 win = (struct reg_window32 *) regs->u_regs[UREG_FP]; in fetch_reg_addr()
136 static unsigned long compute_effective_address(struct pt_regs *regs, in compute_effective_address() argument
152 safe_compute_effective_address(struct pt_regs *regs, unsigned int insn) safe_compute_effective_address() argument
180 do_int_store(int reg_num, int size, unsigned long *dst_addr, struct pt_regs *regs) do_int_store() argument
199 advance(struct pt_regs *regs) advance() argument
215 kernel_mna_trap_fault(struct pt_regs *regs, unsigned int insn) kernel_mna_trap_fault() argument
240 kernel_unaligned_trap(struct pt_regs *regs, unsigned int insn) kernel_unaligned_trap() argument
277 user_unaligned_trap(struct pt_regs *regs, unsigned int insn) user_unaligned_trap() argument
[all...]
/kernel/linux/linux-6.6/arch/riscv/include/asm/
H A Dvector.h24 bool riscv_v_first_use_handler(struct pt_regs *regs);
31 static inline void __riscv_v_vstate_clean(struct pt_regs *regs) in __riscv_v_vstate_clean() argument
33 regs->status = (regs->status & ~SR_VS) | SR_VS_CLEAN; in __riscv_v_vstate_clean()
36 static inline void __riscv_v_vstate_dirty(struct pt_regs *regs) in __riscv_v_vstate_dirty() argument
38 regs->status = (regs->status & ~SR_VS) | SR_VS_DIRTY; in __riscv_v_vstate_dirty()
41 static inline void riscv_v_vstate_off(struct pt_regs *regs) in riscv_v_vstate_off() argument
43 regs->status = (regs in riscv_v_vstate_off()
46 riscv_v_vstate_on(struct pt_regs *regs) riscv_v_vstate_on() argument
51 riscv_v_vstate_query(struct pt_regs *regs) riscv_v_vstate_query() argument
156 riscv_v_vstate_discard(struct pt_regs *regs) riscv_v_vstate_discard() argument
165 riscv_v_vstate_save(struct task_struct *task, struct pt_regs *regs) riscv_v_vstate_save() argument
176 riscv_v_vstate_restore(struct task_struct *task, struct pt_regs *regs) riscv_v_vstate_restore() argument
190 struct pt_regs *regs; __switch_to_vector() local
206 riscv_v_first_use_handler(struct pt_regs *regs) riscv_v_first_use_handler() argument
207 riscv_v_vstate_query(struct pt_regs *regs) riscv_v_vstate_query() argument
[all...]
H A Dptrace.h65 #define user_mode(regs) (((regs)->status & SR_PP) == 0)
70 static inline unsigned long instruction_pointer(struct pt_regs *regs) in instruction_pointer() argument
72 return regs->epc; in instruction_pointer()
74 static inline void instruction_pointer_set(struct pt_regs *regs, in instruction_pointer_set() argument
77 regs->epc = val; in instruction_pointer_set()
80 #define profile_pc(regs) instruction_pointer(regs)
83 static inline unsigned long user_stack_pointer(struct pt_regs *regs) in user_stack_pointer() argument
85 return regs in user_stack_pointer()
87 user_stack_pointer_set(struct pt_regs *regs, unsigned long val) user_stack_pointer_set() argument
94 kernel_stack_pointer(struct pt_regs *regs) kernel_stack_pointer() argument
100 frame_pointer(struct pt_regs *regs) frame_pointer() argument
104 frame_pointer_set(struct pt_regs *regs, unsigned long val) frame_pointer_set() argument
110 regs_return_value(struct pt_regs *regs) regs_return_value() argument
115 regs_set_return_value(struct pt_regs *regs, unsigned long val) regs_set_return_value() argument
137 regs_get_register(struct pt_regs *regs, unsigned int offset) regs_get_register() argument
156 regs_get_kernel_argument(struct pt_regs *regs, unsigned int n) regs_get_kernel_argument() argument
176 regs_irqs_disabled(struct pt_regs *regs) regs_irqs_disabled() argument
[all...]
/kernel/linux/linux-5.10/arch/xtensa/kernel/
H A Dsignal.c54 flush_window_regs_user(struct pt_regs *regs) in flush_window_regs_user() argument
56 const unsigned long ws = regs->windowstart; in flush_window_regs_user()
57 const unsigned long wb = regs->windowbase; in flush_window_regs_user()
65 if (regs->wmask == 1) in flush_window_regs_user()
71 base = (XCHAL_NUM_AREGS / 4) - (regs->wmask >> 4); in flush_window_regs_user()
75 if ((regs->wmask & 2) == 0) in flush_window_regs_user()
76 if (__get_user(sp, (int*)(regs->areg[base * 4 + 1] - 12))) in flush_window_regs_user()
93 &regs->areg[(base + 1) * 4], 16)) in flush_window_regs_user()
99 &regs->areg[(base + 1) * 4], 32)) in flush_window_regs_user()
106 sp = regs in flush_window_regs_user()
134 setup_sigcontext(struct rt_sigframe __user *frame, struct pt_regs *regs) setup_sigcontext() argument
173 restore_sigcontext(struct pt_regs *regs, struct rt_sigframe __user *frame) restore_sigcontext() argument
241 struct pt_regs *regs = current_pt_regs(); xtensa_rt_sigreturn() local
333 setup_frame(struct ksignal *ksig, sigset_t *set, struct pt_regs *regs) setup_frame() argument
425 do_signal(struct pt_regs *regs) do_signal() argument
499 do_notify_resume(struct pt_regs *regs) do_notify_resume() argument
[all...]
/kernel/linux/linux-5.10/arch/nds32/kernel/
H A Dtraps.c65 static void dump_instr(struct pt_regs *regs) in dump_instr() argument
67 unsigned long addr = instruction_pointer(regs); in dump_instr()
164 void die(const char *str, struct pt_regs *regs, int err) in die() argument
176 show_regs(regs); in die()
180 if (!user_mode(regs) || in_interrupt()) { in die()
181 dump_mem("Stack: ", regs->sp, (regs->sp + PAGE_SIZE) & PAGE_MASK); in die()
182 dump_instr(regs); in die()
193 void die_if_kernel(const char *str, struct pt_regs *regs, int err) in die_if_kernel() argument
195 if (user_mode(regs)) in die_if_kernel()
201 bad_syscall(int n, struct pt_regs *regs) bad_syscall() argument
259 send_sigtrap(struct pt_regs *regs, int error_code, int si_code) send_sigtrap() argument
270 do_debug_trap(unsigned long entry, unsigned long addr, unsigned long type, struct pt_regs *regs) do_debug_trap() argument
287 unhandled_interruption(struct pt_regs *regs) unhandled_interruption() argument
296 unhandled_exceptions(unsigned long entry, unsigned long addr, unsigned long type, struct pt_regs *regs) unhandled_exceptions() argument
314 do_dispatch_tlb_misc(unsigned long entry, unsigned long addr, unsigned long type, struct pt_regs *regs) do_dispatch_tlb_misc() argument
325 do_revinsn(struct pt_regs *regs) do_revinsn() argument
338 do_dispatch_general(unsigned long entry, unsigned long addr, unsigned long itype, struct pt_regs *regs, unsigned long oipc) do_dispatch_general() argument
[all...]
/third_party/backends/backend/
H A Drts8891_low.c79 rts8891_write_all (SANE_Int devnum, SANE_Byte * regs, SANE_Int count) in rts8891_write_all() argument
93 sprintf (message + 5 * i, "0x%02x ", regs[i]); in rts8891_write_all()
107 local_regs[j] = regs[i]; in rts8891_write_all()
136 buffer[i + 4] = regs[0xb4 + i]; in rts8891_write_all()
205 rts8891_simple_scan (SANE_Int devnum, SANE_Byte * regs, int regcount, in rts8891_simple_scan() argument
212 rts8891_write_all (devnum, regs, regcount); in rts8891_simple_scan()
414 rts8891_move (struct Rts8891_Device *device, SANE_Byte * regs, in rts8891_move() argument
425 rts8891_set_default_regs (regs); in rts8891_move()
438 regs[0x32] = 0x80; in rts8891_move()
439 regs[ in rts8891_move()
545 rts8891_wait_for_home(struct Rts8891_Device *device, SANE_Byte * regs) rts8891_wait_for_home() argument
596 rts8891_park(struct Rts8891_Device *device, SANE_Byte *regs, SANE_Bool wait) rts8891_park() argument
[all...]
/third_party/mesa3d/src/panfrost/bifrost/
H A Dbi_pack.c72 bi_assign_slot_read(bi_registers *regs, bi_index src) in bi_assign_slot_read() argument
80 if (regs->slot[i] == src.value && regs->enabled[i]) in bi_assign_slot_read()
84 if (regs->slot[2] == src.value && regs->slot23.slot2 == BIFROST_OP_READ) in bi_assign_slot_read()
90 if (!regs->enabled[i]) { in bi_assign_slot_read()
91 regs->slot[i] = src.value; in bi_assign_slot_read()
92 regs->enabled[i] = true; in bi_assign_slot_read()
97 if (!regs->slot23.slot3) { in bi_assign_slot_read()
98 regs in bi_assign_slot_read()
187 bi_pack_registers(bi_registers regs) bi_pack_registers() argument
279 bi_flip_slots(bi_registers *regs) bi_flip_slots() argument
290 bi_get_src_slot(bi_registers *regs, unsigned reg) bi_get_src_slot() argument
303 bi_get_src_new(bi_instr *ins, bi_registers *regs, unsigned s) bi_get_src_new() argument
[all...]
/kernel/linux/linux-5.10/arch/arm64/kernel/
H A Dsyscall.c17 long compat_arm_syscall(struct pt_regs *regs, int scno);
20 static long do_ni_syscall(struct pt_regs *regs, int scno) in do_ni_syscall() argument
25 ret = compat_arm_syscall(regs, scno); in do_ni_syscall()
34 static long __invoke_syscall(struct pt_regs *regs, syscall_fn_t syscall_fn) in __invoke_syscall() argument
36 return syscall_fn(regs); in __invoke_syscall()
39 static void invoke_syscall(struct pt_regs *regs, unsigned int scno, in invoke_syscall() argument
48 ret = __invoke_syscall(regs, syscall_fn); in invoke_syscall()
50 ret = do_ni_syscall(regs, scno); in invoke_syscall()
53 syscall_set_return_value(current, regs, 0, ret); in invoke_syscall()
61 int syscall_trace_enter(struct pt_regs *regs);
93 el0_svc_common(struct pt_regs *regs, int scno, int sc_nr, const syscall_fn_t syscall_table[]) el0_svc_common() argument
191 do_el0_svc(struct pt_regs *regs) do_el0_svc() argument
198 do_el0_svc_compat(struct pt_regs *regs) do_el0_svc_compat() argument
[all...]
/kernel/linux/linux-6.6/arch/loongarch/include/asm/
H A Dsyscall.h24 struct pt_regs *regs) in syscall_get_nr()
26 return regs->regs[11]; in syscall_get_nr()
30 struct pt_regs *regs) in syscall_rollback()
32 regs->regs[4] = regs->orig_a0; in syscall_rollback()
36 struct pt_regs *regs) in syscall_get_error()
38 unsigned long error = regs->regs[ in syscall_get_error()
23 syscall_get_nr(struct task_struct *task, struct pt_regs *regs) syscall_get_nr() argument
29 syscall_rollback(struct task_struct *task, struct pt_regs *regs) syscall_rollback() argument
35 syscall_get_error(struct task_struct *task, struct pt_regs *regs) syscall_get_error() argument
43 syscall_get_return_value(struct task_struct *task, struct pt_regs *regs) syscall_get_return_value() argument
49 syscall_set_return_value(struct task_struct *task, struct pt_regs *regs, int error, long val) syscall_set_return_value() argument
56 syscall_get_arguments(struct task_struct *task, struct pt_regs *regs, unsigned long *args) syscall_get_arguments() argument
69 arch_syscall_is_vdso_sigreturn(struct pt_regs *regs) arch_syscall_is_vdso_sigreturn() argument
[all...]
/kernel/linux/linux-6.6/arch/arm64/include/asm/
H A Dsyscall.h12 typedef long (*syscall_fn_t)(const struct pt_regs *regs);
21 struct pt_regs *regs) in syscall_get_nr()
23 return regs->syscallno; in syscall_get_nr()
27 struct pt_regs *regs) in syscall_rollback()
29 regs->regs[0] = regs->orig_x0; in syscall_rollback()
33 struct pt_regs *regs) in syscall_get_return_value()
35 unsigned long val = regs->regs[ in syscall_get_return_value()
20 syscall_get_nr(struct task_struct *task, struct pt_regs *regs) syscall_get_nr() argument
26 syscall_rollback(struct task_struct *task, struct pt_regs *regs) syscall_rollback() argument
32 syscall_get_return_value(struct task_struct *task, struct pt_regs *regs) syscall_get_return_value() argument
43 syscall_get_error(struct task_struct *task, struct pt_regs *regs) syscall_get_error() argument
51 syscall_set_return_value(struct task_struct *task, struct pt_regs *regs, int error, long val) syscall_set_return_value() argument
66 syscall_get_arguments(struct task_struct *task, struct pt_regs *regs, unsigned long *args) syscall_get_arguments() argument
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/gma500/
H A Doaktrail_device.c182 struct psb_save_area *regs = &dev_priv->regs; in oaktrail_save_display_registers() local
183 struct psb_pipe *p = &regs->pipe[0]; in oaktrail_save_display_registers()
188 regs->psb.saveDSPARB = PSB_RVDC32(DSPARB); in oaktrail_save_display_registers()
189 regs->psb.saveDSPFW1 = PSB_RVDC32(DSPFW1); in oaktrail_save_display_registers()
190 regs->psb.saveDSPFW2 = PSB_RVDC32(DSPFW2); in oaktrail_save_display_registers()
191 regs->psb.saveDSPFW3 = PSB_RVDC32(DSPFW3); in oaktrail_save_display_registers()
192 regs->psb.saveDSPFW4 = PSB_RVDC32(DSPFW4); in oaktrail_save_display_registers()
193 regs->psb.saveDSPFW5 = PSB_RVDC32(DSPFW5); in oaktrail_save_display_registers()
194 regs in oaktrail_save_display_registers()
296 struct psb_save_area *regs = &dev_priv->regs; oaktrail_restore_display_registers() local
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/gma500/
H A Doaktrail_device.c124 struct psb_save_area *regs = &dev_priv->regs; in oaktrail_save_display_registers() local
125 struct psb_pipe *p = &regs->pipe[0]; in oaktrail_save_display_registers()
130 regs->psb.saveDSPARB = PSB_RVDC32(DSPARB); in oaktrail_save_display_registers()
131 regs->psb.saveDSPFW1 = PSB_RVDC32(DSPFW1); in oaktrail_save_display_registers()
132 regs->psb.saveDSPFW2 = PSB_RVDC32(DSPFW2); in oaktrail_save_display_registers()
133 regs->psb.saveDSPFW3 = PSB_RVDC32(DSPFW3); in oaktrail_save_display_registers()
134 regs->psb.saveDSPFW4 = PSB_RVDC32(DSPFW4); in oaktrail_save_display_registers()
135 regs->psb.saveDSPFW5 = PSB_RVDC32(DSPFW5); in oaktrail_save_display_registers()
136 regs in oaktrail_save_display_registers()
238 struct psb_save_area *regs = &dev_priv->regs; oaktrail_restore_display_registers() local
[all...]
/kernel/linux/linux-6.6/arch/s390/kernel/
H A Ddumpstack.c142 static void show_last_breaking_event(struct pt_regs *regs) in show_last_breaking_event() argument
145 printk(" [<%016lx>] ", regs->last_break); in show_last_breaking_event()
146 if (user_mode(regs)) { in show_last_breaking_event()
147 print_vma_addr(KERN_CONT, regs->last_break); in show_last_breaking_event()
150 pr_cont("%pSR\n", (void *)regs->last_break); in show_last_breaking_event()
154 void show_registers(struct pt_regs *regs) in show_registers() argument
156 struct psw_bits *psw = &psw_bits(regs->psw); in show_registers()
159 mode = user_mode(regs) ? "User" : "Krnl"; in show_registers()
160 printk("%s PSW : %px %px", mode, (void *)regs->psw.mask, (void *)regs in show_registers()
179 show_regs(struct pt_regs *regs) show_regs() argument
191 die(struct pt_regs *regs, const char *str) die() argument
[all...]

Completed in 12 milliseconds

12345678910>>...293