aboutsummaryrefslogtreecommitdiff
path: root/kernel/main.c
diff options
context:
space:
mode:
Diffstat (limited to 'kernel/main.c')
-rw-r--r--kernel/main.c7
1 files changed, 2 insertions, 5 deletions
diff --git a/kernel/main.c b/kernel/main.c
index 41619d6..3ed8551 100644
--- a/kernel/main.c
+++ b/kernel/main.c
@@ -5,11 +5,8 @@
#include <fbos/string.h>
#include <fbos/dt.h>
-/*
- * Data related to harts and set by kernel/head.S. Defined in fbos/init.h.
- */
+// Defined in fbos/init.h.
atomic32_t hart_lottery __section(".sdata");
-uint32_t hart_id;
// Defined in fbos/sched.h.
uint64_t stack[STACK_SIZE / sizeof(uint64_t)];
@@ -30,7 +27,7 @@ struct dt_info info = {
.initrd_end = 0,
};
-__noreturn __kernel void start_kernel(void *dtb)
+__noreturn __kernel void start_kernel(uint64_t hart_id, void *dtb)
{
printk("Welcome to FizzBuzz OS!\n");