diff options
| author | Miquel Sabaté Solà <mikisabate@gmail.com> | 2024-11-21 13:09:21 +0100 |
|---|---|---|
| committer | Miquel Sabaté Solà <mikisabate@gmail.com> | 2024-11-21 13:09:21 +0100 |
| commit | 40ffc517e20c381ce8fdb3a881726a26a52e35db (patch) | |
| tree | b969f6e1bc4c400e8c2c8b1d5a18ed75d3f2fd95 /kernel/main.c | |
| parent | d394978a73fce080128dc414e1771d8d89e1e1e0 (diff) | |
| download | fbos-40ffc517e20c.tar.gz fbos-40ffc517e20c.zip | |
Initial parsing of the provided initrd file
We expect a CPIO archive with the 'newc' format for the initrd. Parse
this archive from the given initrd address and fetch the address for
each ELF executable while also pairing which task correspond to which
ELF.
This commit leaves to do the actual parsing of the ELF file for each
task, while also leaving some string utilities to be refined.
Signed-off-by: Miquel Sabaté Solà <mikisabate@gmail.com>
Diffstat (limited to 'kernel/main.c')
| -rw-r--r-- | kernel/main.c | 3 |
1 files changed, 2 insertions, 1 deletions
diff --git a/kernel/main.c b/kernel/main.c index 11f2721..7eb2ef6 100644 --- a/kernel/main.c +++ b/kernel/main.c @@ -20,7 +20,8 @@ __noreturn __kernel void start_kernel(void *dtb) printk("Welcome to FizzBuzz OS!\n"); struct initrd_addr addr = find_dt_initrd_addr(dtb); - __unused(addr); // TODO + + extract_initrd((char *)addr.start, addr.end - addr.start); // TODO: reenable stuff |