/kernel/linux/linux-5.10/arch/sh/include/asm/ |
H A D | elf.h | 102 * 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 D | syscall.h | 21 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 D | exceptions.c | 54 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 D | elf.h | 102 * 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 D | syscall.h | 38 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 D | kgdb.c | 57 { "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 D | kgdb.c | 56 { "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 D | rtc-fm3130.c | 48 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 D | rtc-mpc5121.c | 79 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(®s->second_set, tm->tm_sec); in mpc5121_rtc_update_smh() 93 out_8(®s->minute_set, tm->tm_min); in mpc5121_rtc_update_smh() 94 out_8(®s->hour_set, tm->tm_hour); in mpc5121_rtc_update_smh() 97 out_8(®s->set_time, 0x1); in mpc5121_rtc_update_smh() 98 out_8(®s->set_time, 0x3); in mpc5121_rtc_update_smh() 99 out_8(®s->set_time, 0x1); in mpc5121_rtc_update_smh() 100 out_8(®s->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 D | rtc-fm3130.c | 48 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 D | rtc-mpc5121.c | 77 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(®s->second_set, tm->tm_sec); in mpc5121_rtc_update_smh() 91 out_8(®s->minute_set, tm->tm_min); in mpc5121_rtc_update_smh() 92 out_8(®s->hour_set, tm->tm_hour); in mpc5121_rtc_update_smh() 95 out_8(®s->set_time, 0x1); in mpc5121_rtc_update_smh() 96 out_8(®s->set_time, 0x3); in mpc5121_rtc_update_smh() 97 out_8(®s->set_time, 0x1); in mpc5121_rtc_update_smh() 98 out_8(®s->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 D | traps.c | 52 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 D | unaligned_32.c | 94 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 ®s->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 D | vector.h | 24 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 D | ptrace.h | 65 #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 D | signal.c | 54 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 ®s->areg[(base + 1) * 4], 16)) in flush_window_regs_user() 99 ®s->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 D | traps.c | 65 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 D | rts8891_low.c | 79 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 D | bi_pack.c | 72 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 D | syscall.c | 17 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 D | syscall.h | 24 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 D | syscall.h | 12 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 D | oaktrail_device.c | 182 struct psb_save_area *regs = &dev_priv->regs; in oaktrail_save_display_registers() local 183 struct psb_pipe *p = ®s->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 D | oaktrail_device.c | 124 struct psb_save_area *regs = &dev_priv->regs; in oaktrail_save_display_registers() local 125 struct psb_pipe *p = ®s->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 D | dumpstack.c | 142 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...] |