Demo/Linux_Drivers
1
0
Fork 0
Code Issues Pull Requests Packages Projects Releases Wiki Activity

[linux] porting cvitek asic chips.

Browse Source 
1. update cv182x/cv183x configuration file
	2. update cv181x/cv180x configuration file
	3. update clk driver for cvitek
	4. update dma driver for cvitek
	5. update soc driver for cvitek
	6. porting cvitek ion driver from kernel-4.19
	7. compatible with riscv

Change-Id: Icff9fafe0ebe7d6bab824bbadb952e08bdc66c19
This commit is contained in:
wangliang.wang
2023-03-09 14:38:25 +08:00
committed by sam.xiang
parent 4bc998a131
commit 4f810186ab
2062 changed files with 544892 additions and 2134 deletions
Download Patch File Download Diff File Expand all files Collapse all files

24
linux_5.10/arch/riscv/include/asm/processor.h
View File

@ -19,7 +19,11 @@
#define TASK_UNMAPPED_BASE PAGE_ALIGN(TASK_SIZE / 3)
#define STACK_TOP TASK_SIZE
#ifdef CONFIG_64BIT
#define STACK_TOP_MAX TASK_SIZE_64
#else
#define STACK_TOP_MAX STACK_TOP
#endif
#define STACK_ALIGN 16
#ifndef __ASSEMBLY__
@ -27,6 +31,15 @@
struct task_struct;
struct pt_regs;
#ifdef CONFIG_VECTOR_EMU
struct vsetvl_info {
unsigned long last_vector_pc;
unsigned long regid;
unsigned long vl;
unsigned long vtype;
};
#endif
/* CPU-specific state of a task */
struct thread_struct {
/* Callee-saved registers */
@ -34,6 +47,11 @@ struct thread_struct {
unsigned long sp; /* Kernel mode stack */
unsigned long s[12]; /* s[0]: frame pointer */
struct __riscv_d_ext_state fstate;
unsigned long bad_cause;
struct __riscv_v_state vstate;
#ifdef CONFIG_VECTOR_EMU
struct vsetvl_info vsetvl_state;
#endif
};
#define INIT_THREAD { \
@ -52,6 +70,12 @@ struct thread_struct {
extern void start_thread(struct pt_regs *regs,
unsigned long pc, unsigned long sp);
#ifdef CONFIG_COMPAT
#define DEFAULT_MAP_WINDOW_64 TASK_SIZE_64
#else
#define DEFAULT_MAP_WINDOW_64 TASK_SIZE
#endif
/* Free all resources held by a thread. */
static inline void release_thread(struct task_struct *dead_task)
{