/linux/arch/arm64/kernel/ |
H A 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 …]
|
/linux/drivers/media/platform/samsung/s5p-jpeg/ |
H A 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 …]
|
/linux/arch/arm/include/asm/ |
H A 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/kernel/entry/ |
H A 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/arch/csky/include/asm/ |
H A 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/arch/csky/kernel/probes/ |
H A 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/arch/loongarch/include/asm/ |
H A 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/arch/mips/kernel/ |
H A 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/arch/sparc/include/asm/ |
H A 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 …]
|
H A 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/arch/mips/include/asm/ |
H A 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/arch/powerpc/include/asm/ |
H A 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/arch/riscv/kernel/ |
H A 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 …]
|
H A D | signal.c | 42 static long restore_fp_state(struct pt_regs *regs, in restore_fp_state() 56 static long save_fp_state(struct pt_regs *regs, in save_fp_state() 67 #define save_fp_state(task, regs) (0) argument 68 #define restore_fp_state(task, regs) (0) argument 73 static long save_v_state(struct pt_regs *regs, void __user **sc_vec) in save_v_state() 116 static long __restore_v_state(struct pt_regs *regs, void __user *sc_vec) in __restore_v_state() 146 #define save_v_state(task, regs) (0) argument 147 #define __restore_v_state(task, regs) (0) argument 150 static long restore_sigcontext(struct pt_regs *regs, in restore_sigcontext() 233 struct pt_regs *regs = current_pt_regs(); in SYSCALL_DEFINE0() local [all …]
|
/linux/arch/arm64/kernel/probes/ |
H A 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/arch/powerpc/kernel/ |
H A 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/arch/hexagon/kernel/ |
H A 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/arch/arm/probes/kprobes/ |
H A 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/arch/x86/lib/ |
H A 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/arch/sh/include/asm/ |
H A 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/arch/riscv/include/asm/ |
H A D | vector.h | 44 static inline void __riscv_v_vstate_clean(struct pt_regs *regs) in __riscv_v_vstate_clean() 49 static inline void __riscv_v_vstate_dirty(struct pt_regs *regs) in __riscv_v_vstate_dirty() 54 static inline void riscv_v_vstate_off(struct pt_regs *regs) in riscv_v_vstate_off() 59 static inline void riscv_v_vstate_on(struct pt_regs *regs) in riscv_v_vstate_on() 64 static inline bool riscv_v_vstate_query(struct pt_regs *regs) in riscv_v_vstate_query() 169 static inline void riscv_v_vstate_discard(struct pt_regs *regs) in riscv_v_vstate_discard() 179 struct pt_regs *regs) in riscv_v_vstate_save() 188 struct pt_regs *regs) in riscv_v_vstate_restore() 197 struct pt_regs *regs) in riscv_v_vstate_set_restore() 244 struct pt_regs *regs; in __switch_to_vector() local [all …]
|
/linux/arch/x86/mm/ |
H A D | extable.c | 16 static inline unsigned long *pt_regs_nr(struct pt_regs *regs, int nr) in pt_regs_nr() 34 struct pt_regs *regs) in ex_handler_default() 58 struct pt_regs *regs, in ex_handler_zeropad() 99 struct pt_regs *regs, int trapnr) in ex_handler_fault() 106 struct pt_regs *regs, int trapnr) in ex_handler_sgx() 123 struct pt_regs *regs) in ex_handler_fprestore() 159 struct pt_regs *regs, int trapnr, in ex_handler_uaccess() 168 struct pt_regs *regs, bool wrmsr, bool safe, int reg) in ex_handler_msr() 196 struct pt_regs *regs) in ex_handler_clear_fs() 205 struct pt_regs *regs, int reg, int imm) in ex_handler_imm_reg() [all …]
|
/linux/arch/x86/entry/ |
H A D | common.c | 42 static __always_inline bool do_syscall_x64(struct pt_regs *regs, int nr) in do_syscall_x64() 58 static __always_inline bool do_syscall_x32(struct pt_regs *regs, int nr) in do_syscall_x32() 76 __visible noinstr bool do_syscall_64(struct pt_regs *regs, int nr) in do_syscall_64() 134 static __always_inline int syscall_32_enter(struct pt_regs *regs) in syscall_32_enter() 155 static __always_inline void do_syscall_32_irqs_on(struct pt_regs *regs, int nr) in do_syscall_32_irqs_on() 210 __visible noinstr void do_int80_emulation(struct pt_regs *regs) in do_int80_emulation() 326 __visible noinstr void do_int80_syscall_32(struct pt_regs *regs) in do_int80_syscall_32() 346 static noinstr bool __do_fast_syscall_32(struct pt_regs *regs) in __do_fast_syscall_32() 394 __visible noinstr bool do_fast_syscall_32(struct pt_regs *regs) in do_fast_syscall_32() 441 __visible noinstr bool do_SYSENTER_32(struct pt_regs *regs) in do_SYSENTER_32() [all …]
|
H A D | entry_fred.c | 21 static noinstr void fred_bad_type(struct pt_regs *regs, unsigned long error_code) in fred_bad_type() 54 static noinstr void fred_intx(struct pt_regs *regs) in fred_intx() 78 static __always_inline void fred_other(struct pt_regs *regs) in fred_other() 138 static noinstr void fred_handle_spurious_interrupt(struct pt_regs *regs) in fred_handle_spurious_interrupt() 159 static noinstr void fred_extint(struct pt_regs *regs) in fred_extint() 180 static noinstr void fred_hwexc(struct pt_regs *regs, unsigned long error_code) in fred_hwexc() 215 static noinstr void fred_swexc(struct pt_regs *regs, unsigned long error_code) in fred_swexc() 224 __visible noinstr void fred_entry_from_user(struct pt_regs *regs) in fred_entry_from_user() 256 __visible noinstr void fred_entry_from_kernel(struct pt_regs *regs) in fred_entry_from_kernel() 285 __visible noinstr void __fred_entry_from_kvm(struct pt_regs *regs) in __fred_entry_from_kvm()
|
/linux/drivers/scsi/mvsas/ |
H A D | mv_64xx.c | 16 void __iomem *regs = mvi->regs; in mvs_64xx_detect_porttype() local 30 void __iomem *regs = mvi->regs; in mvs_64xx_enable_xmt() local 43 void __iomem *regs = mvi->regs; in mvs_64xx_phy_hacks() local 69 void __iomem *regs = mvi->regs; in mvs_64xx_stp_reset() local 126 void __iomem *regs = mvi->regs; in mvs_64xx_clear_srs_irq() local 146 void __iomem *regs = mvi->regs; in mvs_64xx_chip_reset() local 196 void __iomem *regs = mvi->regs; in mvs_64xx_phy_disable() local 218 void __iomem *regs = mvi->regs; in mvs_64xx_phy_enable() local 240 void __iomem *regs = mvi->regs; in mvs_64xx_init() local 422 void __iomem *regs = mvi->regs; in mvs_64xx_interrupt_enable() local [all …]
|