From f560a5312f524caaa427f4f548b97ab3f32904b8 Mon Sep 17 00:00:00 2001 From: Miquel Sabaté Solà Date: Sat, 30 Nov 2024 22:28:51 +0100 Subject: Rename 'switch_to' to 'set_return_address_to' MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit The original name came from a previous hack the did not work but somehow the old name remained. Now it was more misleading than anything else, so let's rename it to something that is closer to what it actually does. Signed-off-by: Miquel Sabaté Solà --- kernel/trap.c | 9 ++++----- 1 file changed, 4 insertions(+), 5 deletions(-) (limited to 'kernel') diff --git a/kernel/trap.c b/kernel/trap.c index f98fcc7..4e31b6d 100644 --- a/kernel/trap.c +++ b/kernel/trap.c @@ -78,7 +78,7 @@ __aligned(4) __s_interrupt __kernel void interrupt_handler(void) if (IS_EXCEPTION(cause)) { exception_handler(cause); - switch_to(TASK_INIT); + set_return_address_to(TASK_INIT); goto end; } @@ -94,12 +94,11 @@ __aligned(4) __s_interrupt __kernel void interrupt_handler(void) // BEHOLD! The fizz buzz logic! :D seconds_elapsed += 1; if ((seconds_elapsed % 15) == 0) { - switch_to(TASK_FIZZBUZZ); + set_return_address_to(TASK_FIZZBUZZ); } else if ((seconds_elapsed % 5) == 0) { - switch_to(TASK_BUZZ); + set_return_address_to(TASK_BUZZ); } else if ((seconds_elapsed % 3) == 0) { - switch_to(TASK_FIZZ); - } else { + set_return_address_to(TASK_FIZZ); } // Re-enable timer interrupts. -- cgit v1.2.3