From 7b1b8ebb48174445083bc7fa336dc00619cbf126 Mon Sep 17 00:00:00 2001 From: Miquel Sabaté Solà Date: Mon, 2 Dec 2024 21:06:39 +0100 Subject: Don't repeat the task name when printing the model MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit When printing the initial model message on DEBUG it repeated the "init" message twice. Avoid that by directly using 'write' on some of the calls. Fixes: 32e880127366 ("Prepend the name of the task on debug") Signed-off-by: Miquel Sabaté Solà --- kernel/main.c | 5 +++-- 1 file changed, 3 insertions(+), 2 deletions(-) (limited to 'kernel/main.c') diff --git a/kernel/main.c b/kernel/main.c index 19220f6..3d2b524 100644 --- a/kernel/main.c +++ b/kernel/main.c @@ -2,6 +2,7 @@ #include #include #include +#include #include // Stack to be used by our processes. "Blasphemy!" I hear you say. "How dare you @@ -46,8 +47,8 @@ __noreturn __kernel void start_kernel(void *dtb) // If we were able to fetch the model, print it now. if (info.model[0] != '\0') { printk("Running on: "); - printk(info.model); - printk("\n"); + write(info.model, strlen(info.model)); + write("\n", 1); } // At this point everything has already been handled: setup the interrupt -- cgit v1.2.3