Home
last modified time | relevance | path

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

/linux/arch/riscv/include/asm/
H A Dvector.h27 if (has_xtheadvector()) \
36 if (has_xtheadvector()) \
74 static __always_inline bool has_xtheadvector(void) in has_xtheadvector() function
110 if (has_xtheadvector()) in riscv_v_enable()
118 if (has_xtheadvector()) in riscv_v_disable()
138 if (has_xtheadvector()) { in __vstate_csr_save()
177 if (has_xtheadvector()) { in __vstate_csr_restore()
203 if (has_xtheadvector()) { in __riscv_v_vstate_save()
239 if (has_xtheadvector()) { in __riscv_v_vstate_restore()
275 if (has_xtheadvector()) in __riscv_v_vstate_discard()
[all …]
H A Dswitch_to.h120 if (has_vector() || has_xtheadvector()) \
/linux/arch/riscv/kernel/
H A Dvector.c66 if (!(has_vector() || has_xtheadvector())) in riscv_v_setup_ctx_cache()
188 if (!(has_vector() || has_xtheadvector())) in riscv_v_first_use_handler()
231 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_init()
253 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_get_current()
264 if (!(has_vector() || has_xtheadvector())) in riscv_v_vstate_ctrl_set_current()
314 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.c78 !((has_vector() || has_xtheadvector()) && in save_v_state()
199 if (!(has_vector() || has_xtheadvector()) || !riscv_v_vstate_query(regs) || in restore_sigcontext()
221 if (has_vector() || has_xtheadvector()) { in get_rt_frame_size()
H A Dprocess.c196 if (has_vector() || has_xtheadvector()) in arch_release_task_struct()
259 if (has_vector() || has_xtheadvector()) in copy_thread()
H A Dptrace.c159 if (!(has_vector() || has_xtheadvector())) in riscv_vr_active()