Home
last modified time | relevance | path

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

/arch/riscv/include/asm/
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()
137 if (has_xtheadvector()) { in __vstate_csr_save()
176 if (has_xtheadvector()) { in __vstate_csr_restore()
202 if (has_xtheadvector()) { in __riscv_v_vstate_save()
238 if (has_xtheadvector()) { in __riscv_v_vstate_restore()
274 if (has_xtheadvector()) in __riscv_v_vstate_discard()
[all …]
A Dswitch_to.h120 if (has_vector() || has_xtheadvector()) \
/arch/riscv/kernel/
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()
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()
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()
A Dprocess.c196 if (has_vector() || has_xtheadvector()) in arch_release_task_struct()
259 if (has_vector() || has_xtheadvector()) in copy_thread()

Completed in 12 milliseconds