diff options
| author | Miquel Sabaté Solà <mikisabate@gmail.com> | 2024-11-20 11:43:08 +0100 |
|---|---|---|
| committer | Miquel Sabaté Solà <mikisabate@gmail.com> | 2024-11-20 11:43:08 +0100 |
| commit | fb9627cc985912a57de8b4bedc98991e290e4075 (patch) | |
| tree | b7f0f72df6c6feb6beb672523afde5f793c87755 /kernel/main.c | |
| parent | d3afdd9284f7e9838fbde4c941193ec2032d6a26 (diff) | |
| download | fbos-fb9627cc985912a57de8b4bedc98991e290e4075.tar.gz fbos-fb9627cc985912a57de8b4bedc98991e290e4075.zip | |
Fetch the initrd address from the DTB blob
The kernel entry has a pointer to the DTB blob as a parameter. From this
pointer we can parse the the DTB blob to find the properties
"chosen->linux,initrd-start" and "chosen->linux,initrd-start". These
properties are guaranteed to have 64-bit addresses which point where the
initrd is in memory, which we need to fetch the binaries to be loaded.
Signed-off-by: Miquel Sabaté Solà <mikisabate@gmail.com>
Diffstat (limited to 'kernel/main.c')
| -rw-r--r-- | kernel/main.c | 5 |
1 files changed, 3 insertions, 2 deletions
diff --git a/kernel/main.c b/kernel/main.c index 07188b9..11f2721 100644 --- a/kernel/main.c +++ b/kernel/main.c @@ -13,13 +13,14 @@ struct task_struct init_task = { .stack = init_stack }; * function can (and will) assume that everything has been reset and that we can * start the whole thing. */ -__noreturn __kernel void start_kernel(uintptr_t *dtb) +__noreturn __kernel void start_kernel(void *dtb) { // TODO: disable irqs, etc. printk("Welcome to FizzBuzz OS!\n"); - parse_dtb(dtb); + struct initrd_addr addr = find_dt_initrd_addr(dtb); + __unused(addr); // TODO // TODO: reenable stuff |