aboutsummaryrefslogtreecommitdiff
path: root/riscv/include/uapi/asm/sigcontext.h
diff options
context:
space:
mode:
authorPasha <pasha@member.fsf.org>2024-02-20 18:55:36 +0000
committerPasha <pasha@member.fsf.org>2024-02-20 18:55:36 +0000
commit6fca8abef7e6d7be1a9e6d93dd0f2b7fbc5b28e5 (patch)
tree9f5ccbaa6ec19ff5a42d9b3cde01f739e1d7c77d /riscv/include/uapi/asm/sigcontext.h
parent5e0b8d508ed51004bd836384293be00950ee62c9 (diff)
downloadgnumach-riscv-6fca8abef7e6d7be1a9e6d93dd0f2b7fbc5b28e5.tar.gz
gnumach-riscv-6fca8abef7e6d7be1a9e6d93dd0f2b7fbc5b28e5.tar.bz2
initial risc-v exampleHEADmaster
Diffstat (limited to 'riscv/include/uapi/asm/sigcontext.h')
-rw-r--r--riscv/include/uapi/asm/sigcontext.h40
1 files changed, 40 insertions, 0 deletions
diff --git a/riscv/include/uapi/asm/sigcontext.h b/riscv/include/uapi/asm/sigcontext.h
new file mode 100644
index 0000000..cd4f175
--- /dev/null
+++ b/riscv/include/uapi/asm/sigcontext.h
@@ -0,0 +1,40 @@
+/* SPDX-License-Identifier: GPL-2.0-only WITH Linux-syscall-note */
+/*
+ * Copyright (C) 2012 Regents of the University of California
+ */
+
+#ifndef _UAPI_ASM_RISCV_SIGCONTEXT_H
+#define _UAPI_ASM_RISCV_SIGCONTEXT_H
+
+#include <asm/ptrace.h>
+
+/* The Magic number for signal context frame header. */
+#define RISCV_V_MAGIC 0x53465457
+#define END_MAGIC 0x0
+
+/* The size of END signal context header. */
+#define END_HDR_SIZE 0x0
+
+#ifndef __ASSEMBLY__
+
+struct __sc_riscv_v_state {
+ struct __riscv_v_ext_state v_state;
+} __attribute__((aligned(16)));
+
+/*
+ * Signal context structure
+ *
+ * This contains the context saved before a signal handler is invoked;
+ * it is restored by sys_rt_sigreturn.
+ */
+struct sigcontext {
+ struct user_regs_struct sc_regs;
+ union {
+ union __riscv_fp_state sc_fpregs;
+ struct __riscv_extra_ext_header sc_extdesc;
+ };
+};
+
+#endif /*!__ASSEMBLY__*/
+
+#endif /* _UAPI_ASM_RISCV_SIGCONTEXT_H */