Home
last modified time | relevance | path

Searched refs:has_xtheadvector (Results 1 – 6 of 6) sorted by relevance

/linux-6.15/arch/riscv/include/asm/
H A Dvector.h27 if (has_xtheadvector()) \
36 if (has_xtheadvector()) \
73 static __always_inline bool has_xtheadvector(void) in has_xtheadvector() function
109 if (has_xtheadvector()) in riscv_v_enable()
117 if (has_xtheadvector()) in riscv_v_disable()
132 if (has_xtheadvector()) { in __vstate_csr_save()
171 if (has_xtheadvector()) { in __vstate_csr_restore()
197 if (has_xtheadvector()) { in __riscv_v_vstate_save()
233 if (has_xtheadvector()) { in __riscv_v_vstate_restore()
269 if (has_xtheadvector()) in __riscv_v_vstate_discard()
[all …]
H A Dswitch_to.h120 if (has_vector() || has_xtheadvector()) \
/linux-6.15/arch/riscv/kernel/
H A Dvector.c66 if (!(has_vector() || has_xtheadvector())) in riscv_v_setup_ctx_cache()
186 if (!(has_vector() || has_xtheadvector())) in riscv_v_first_use_handler()
229 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_init()
251 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_get_current()
262 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_set_current()
312 if (has_vector() || has_xtheadvector()) in riscv_v_sysctl_init()
H A Dkernel_mode_vector.c211 if (WARN_ON(!(has_vector() || has_xtheadvector()))) in kernel_vector_begin()
239 if (WARN_ON(!(has_vector() || has_xtheadvector()))) in kernel_vector_end()
H A Dsignal.c192 if (!(has_vector() || has_xtheadvector()) || !riscv_v_vstate_query(regs) || in restore_sigcontext()
214 if (has_vector() || has_xtheadvector()) { in get_rt_frame_size()
281 if ((has_vector() || has_xtheadvector()) && riscv_v_vstate_query(regs)) in setup_sigcontext()
H A Dprocess.c193 if (has_vector() || has_xtheadvector()) in arch_release_task_struct()
243 if (has_vector() || has_xtheadvector()) in copy_thread()