The Flopperating System (tfos) - x86 32 bit Hobby OS

[bold grove]

Implemented sys_print

[bold grove]

Happy 20

Happy 20!

[simple vault]

Charge ur phone 🙏
Anyways, how long have you worked on floppaos?

[elfin basin]

1% battery is scary

[primal nymph]

nah, it's at least 1 more hour

(if it's an adroid)

a few seconds with iphone

lol

[radiant grove]

moneyay 🔥 🔥 🔥 🔥

[bold grove]

about a year and a month

so 13 months

[radiant grove]

floppa os is 13 years old :0

[bold grove]

Pmm rewrite may actually be due

[radiant grove]

oh no

41st pmm rewrite
59th vmm rewrite
54th scheduler rewrite

[bold grove]

My new allocation technique is now done

Not my pmm, my heap is now done

Im working on pmm rn

[bold grove]

There’s a bug in proc_create_init_process()

[radiant grove]

:(

awh

REWRITE THE FUNCTION!!!

[bold grove]

I am doing that

[ivory blade]

yo

[bold grove]

god this stupid fucking bug

@eternal epoch can u help me

im able to allocate anywhere else in the kernel besides in my sched_internal_init_thread_stack_alloc

any idea as to why i cant allocate only within one function

LETS FUCKING GO

I FIXED THE BUG

AYAROTHWFADWGDFOSBFVRDADSULFADSLF

THAT WAS 4 HOURS OF DEBUGGING

[paper cloak]

What was it

[bold grove]

vmm_alloc returning bogus value when mapping to the kernel region

@paper cloak i switched to a new allocator type and removed slab

wanted something unique

[paper cloak]

so you don't know what was the bug

[bold grove]

https://github.com/amar454/The-Flopperating-System/blob/main/mem/alloc.c

[bold grove]

my vmm_alloc returns (uintptr_t)-1 on error, not 0, and i was checking for 0 instead of (uintptr_t)-1 , which was why it said the allocation failed

[paper cloak]

Ahh fun

[paper cloak]

That just looks like a bad bitmap allocator or something

[bold grove]

no, its deeper than that

basically a box is a page

when requesting an alloc, it combines 32 byte blocks until the allocation size is fufilled

[paper cloak]

It's not, you check for free memory by scanning O(n)

[bold grove]

oh

so i guess its just a bitmap then

but its more unique i guess

and its pretty fast

[paper cloak]

It's worse because you don't actually use a bitmap

You store a byte in every block or whatever

[bold grove]

yes

how could i make it better

[paper cloak]

So you waste like 128 bytes instead of 128 bits

I wouldn't do that at all, at least use a free list

Then it's just shitty slab

[radiant grove]

memory rewrite number [insert large number]

[paper cloak]

Kernel heap allocation is already solved!! Use a proper slab allocator

(it's not but a proper slab allocator is pretty damn good)

[bold grove]

i mean i had slab before

i just wanted something different

i guess

i implemented kmem months ago

[bold grove]

Yes

[radiant grove]

2^32

[bold grove]

I definitely spent more than 10 hours debugging My stupid init process creation function

Looking back having a seperate allocator for heap allocations over page size was a dumbass idea

[radiant grove]

RIP

[bold grove]

amarat in april 2025 was a fucking idiot

[radiant grove]

amarat from april 2025 reciprocates the feeling towards amarat from december 2025

[bold grove]

the wackiest month was fucking january

[radiant grove]

tf happened?

[bold grove]

i vibe coded alot and didnt understand shit

the gdt was hard for me back then believe it or not

[radiant grove]

[radiant grove]

insanity

[bold grove]

😎

[radiant grove]

fopaerating system™

why is paging brown

is it evil

[bold grove]

yes.

idk actually why its brown

[radiant grove]

nullium ptsd

[bold grove]

Kvass: the return of the GDT

[radiant grove]

i swear when i get to that point im playing doom eternal with the page tables it made my sanity explode

[rigid root]

Letsgo

[bold grove]

mr uacpi!!!

changed 4 lines of code!

nice...

[rigid root]

Now change 5 lines

[bold grove]

That would blow up everything

[rigid root]

☠️

[bold grove]

FloppaOS stable kernel!

I did fix the issue tho

And now i print the memmap

:)

@high hawk look!!

sorry for ping but im just excited

[high hawk]

what happened?

[bold grove]

i print the memmap now and i made my own heap allocator

[high hawk]

nice!

[bold grove]

and i fixed my init process farting everywhere

[high hawk]

what kind of heap allocator did you implement?

[bold grove]

my own

basically i lazily allocate pages and make them "boxes"

each box is made up of 32 byte blocks

and i combine blocks until the size of the allocation is satisfied

then i combine the blocks into an "object" and return a void pointer to the object

ive consumed many caffeinated beverages

[bold grove]

is it valid?

[high hawk]

it depends

firstly on your definition of valid

and secondly, on how exactly you implemented this

[high hawk]

how do you keep track of which blocks are free and which are occupied?

[bold grove]

each block has a boolean field

[high hawk]

so it's basically a bitmap allocator of 32 byte blocks?

[bold grove]

something like that yeah

[high hawk]

I suppose it's ok

many people do worse allocators

[bold grove]

i just wanted something easy to understand and unique, i guess thats what i mean when i ask if its valid

[high hawk]

if you have allocations much larger than 32 bytes, it will have to scan a lot to find a sequence of free blocks

and if you have a lot of allocations of different sizes, this will lead to external fragmentation

[bold grove]

true, i didnt think of that

[high hawk]

if almost all of your allocations are 32 bytes, it's fine tho

secondly

[high hawk]

the bool field takes up 1 byte

you could store 8 such flags in per byte if you have a bitmap

[bold grove]

So it would be better if I stored a byte rather than a Boolean?

[high hawk]

instead of having a bool (which has the same size as a uint8_t) per block, you could have 8 blocks per uint8_t, and then use bitwise operations to extract the flags

[bold grove]

Ohhhhhh

I see what you mean

Lemme implement that

Maybe after I take a break first

I’ve been locked in all day

@high hawk i implemented what you said

i was able to get rid of the whole block_t struct too

just using a bitmap within my box_t

[high hawk]

nice

[bold grove]

this is what my box alloc looks like now

[radiant grove]

when is floppaos getting rewritten in rust (its gonna be blazing fast 🚀)

[bold grove]

Absolutely never

Fuck rust

Way too complicated for my smooth brain

[radiant grove]

you passed the test

i just made it up

there was no test until 3.14 seconds before

[bold grove]

Lowkey so much OSdev has made me a much better programmer

[bold grove]

FloppaOS is already blazing fast lowkey

[radiant grove]

c isnt blazing fast 🚀 enough, you need rust to become actually blazing fast 🚀

[bold grove]

I hope that’s sarcasm

[radiant grove]

im legally obliged to put a rocket emoji

[radiant grove]

it is

unless 🚀

[bold grove]

FloppaOS will never be written in Rust

c only

Like deadass

The new heap allocator seems to be pretty fast honestly

I can allocate like 3gb instantly

Idk why I’d need to allocate that much

[radiant grove]

google chrome

jk floppaos will obviously have a netscape fork

[bold grove]

or no browser

i dont really need a browser for the goals of this os

[radiant grove]

fair

[bold grove]

i made actual signals 😎

@hasty anchor sorry for the ping but is this a solid signal implementation? obviously not fully featured but is it valid

[hasty anchor]

not really, I recommend reading more about how signals work

they are very finnicky and annoying to get right

[bold grove]

okay thank you ill do that

[bold grove]

I should make a dispatch table right?

For shit like SIGINT, etc

Sigint being a graceful exit

[hasty anchor]

think of them like userspace interrupts, where certain events (like a bad page fault) can send a non-maskable signal or other processes (or itself) can send signals that will be handled at some point in the future

[bold grove]

I see

Sounds like a pain in the ass to implement

[paper cloak]

Why do you lock this but no lock in the allocator

[torpid viper]

SIGSEGV is non maskable ?

i belive posix say masking SIGSEGV is ud

oh maybee you were talking about SIGKILL and SIGSTOP

[bold grove]

I lock around box_alloc() in kmalloc()

[bold grove]

Working on signals rn

Read up on them more

1am code sesh

[ebon mirage]

pay close attention to the fine print around SIGTSTP and SIGCONT 😭
I hear they're very special and indeed I think I handle them incorrectly myself and will have to fix that, so yeah if something feels odd with those, I feel you

[elfin basin]

I died at 3 am

How long did you stay up

[bold grove]

3 as well

[bold grove]

i think i got it right

pushed all the signal stuff

also i switched to a new text editor

[rigid root]

people before compiler atomics were invented

[violet anchor]

2009?

my code had atomics like that

[bold grove]

Yeah I’m using builtins now

[bold grove]

mutexes added

[radiant grove]

mootex

[hasty anchor]

Thats some spooky non atomic code

[bold grove]

It’s fixed now

Finally using a macro for my isr stub

[elfin basin]

This is one of the few 32bit OS’s that isn’t garbage

Most are copy and paste from tutorial

No soul

No special

Some times not even a OS and just an extremely bad shell

[bold grove]

Thank you so much, this means a lot

[paper cloak]

turnstile when

[bold grove]

When I read up on them

[paper cloak]

Solaris internals

[bold grove]

I’m gonna make an early memory allocator

Just a free list of pages

[bold grove]

void mutex_lock(mutex_t* mutex, process_t* owner) {
    thread_t* current = current_thread;

    for (;;) {
        int expected = MUTEX_UNLOCKED;

        // wait for mutex to be unlocked
        if (atomic_compare_exchange_strong_explicit(
                &mutex->state, &expected, MUTEX_LOCKED, memory_order_acquire, memory_order_relaxed)) {
            mutex->owner = owner;
            return;
        }

        spinlock(&mutex->wait_lock);

        // if mutex is unlocked, unlock wait_lock and try again
        if (atomic_load_explicit(&mutex->state, memory_order_relaxed) == MUTEX_UNLOCKED) {
            spinlock_unlock(&mutex->wait_lock, true);
            continue;
        }

        // add to mutex wait queue
        sched_thread_list_add(current, &mutex->wait_queue);

        spinlock_unlock(&mutex->wait_lock, true);

        // sets thread state to blocked
        sched_block();
    }
}

Here’s the final form

[crimson plover]

still got that race condition between spinlock_unlock and sched_block

[bold grove]

Redid my interrupts

[radiant grove]

NO THE REWRITES ARE ESCAPING MEMORY MANAGEMENT

[static tartan]

yo ur also making an OS in protected mode? 🔥

[bold grove]

Yes

But the mutex isn’t arch specific

[static tartan]

epik
could u ⭐ my post (coz i ⭐'d urs tehehe)

[bold grove]

Yes send it

[static tartan]

send?

[bold grove]

Send the chat. But I found it

Star my repo and I’ll star yours

[static tartan]

i did

[bold grove]

https://github.com/amar454

Send me your repo

[static tartan]

it's in the chat

but ok

[bold grove]

I starred it https://github.com/amar454/The-Flopperating-System

[static tartan]

https://github.com/geiger-games/termOS

[bold grove]

Nice

adding pushlocks

@paper cloak pushlock gang

[paper cloak]

why not turnstiles

[bold grove]

Push lock better

[paper cloak]

No

turnstiles provide an easy way to do PI

[bold grove]

Idk what that is, I’ll look it up

[bold grove]

@paper cloak

here is my turnstile, what else does it need

i actually made it more sophisticated

Added priority handling within

[paper cloak]

this is not a turnstile 🥀 💀 💔

[elfin basin]

What is it then

Tuna?

[bold grove]

I fixed it

[paper cloak]

What does it look like now

[bold grove]

https://github.com/amar454/The-Flopperating-System/blob/main/task/sync/turnstile.h

[paper cloak]

still not

[quaint onyx]

Your name uses an posix reserved identifier.

[crimson plover]

his kernel isnt using posix

its a freestanding environment

there is no posix

[quaint onyx]

https://cdn.discordapp.com/attachments/1075161036258279515/1409279949348671488/XHq0W8bya7euNbcF.gif

[crimson plover]

his names are probably violating 50000 other standards

who cares if he is not using them

[hasty anchor]

I do the same never ran into issues

[quaint onyx]

well I cause ub all the time and also never ran into issues but one day you might.

[hasty anchor]

Me when I use names reserved by posix in a non-posix environment

Thats like saying you cant define some windows reserved type on linux because its reserved on windows

[quaint onyx]

well I guess you missed the talk in osdev misc 0 but I was talking about posix environments.

[radiant grove]

you dont have to abide by the rules of something that you dont want to comply with

[crimson plover]

yes but here you arent

you explicitly replied to a url of a kernel

[quaint onyx]

No.

I explicitly mentioned his name in a jokeful manner.

You started tunnel visioning on his kernel.

[crimson plover]

well excuse me for assuming you were refering to the turnstile typedef in his kernel as you replied to the url that points to it and which his name is a reference of

[quaint onyx]

You are excused.

[elfin basin]

UB is good for you

UB being bad is a lie made up by the CIA

dont use Rust

stick to writing raw machine code in a hex editor

its the best way

UB and memory issues are your best friend

the issues part is also a lie

made by the CIA

its actually memory lovely issues

remember kids

UB and memory issues are lovely and safe

don't listen to that CIA agent

listening on your chat messages and phone calls

evil

[bold grove]

Most sane Flopperating system thread conversation

[bold grove]

Anyways

Turnstile work going on

[crimson plover]

https://tenor.com/view/rust-rust-lang-ferris-programming-jarvis-gif-7441835028842397805

[azure rapids]

yeah when you write perfect code it's how the cia writes code so they can figure out your code and steal it

always add ub

[bold grove]

made an init system

[simple vault]

Fire

[bold grove]

@paper cloak I did turnstiles I think

Added PI

https://github.com/amar454/The-Flopperating-System/blob/main/task/sync/turnstile.h

[paper cloak]

That's much better but there's some stuff that's just plain wrong

Your locking in particular is wrong I'm pretty sure

Also looking through every turnstile to find yours is... questionable

[bold grove]

making an early memory allocator

idk what i will use it for

but itll exist

[bold grove]

new logo!

[bold grove]

@paper cloak day 3 of tryna do turnstiles

https://github.com/amar454/The-Flopperating-System/blob/main/task/sync/turnstile.h

[paper cloak]

You should look at Solaris

[static tartan]

flopperation
i love it
just rolls off the tongue

[radiant grove]

the scroll contains the rewrites

[crimson plover]

its the dragon scroll

[bold grove]

made an ata driver

i just used port i/o

didnt wanna deal wit the ahci bullshit

https://github.com/amar454/The-Flopperating-System/blob/main/drivers/ata/ata.c

i need to add locks to this though

[radiant grove]

ata

[foggy cedar]

Pio is the slowest thing in existence if you're running under KVM btw

And it doesn't take long to realize why

[bold grove]

I’m not so

[foggy cedar]

You should still look into DMA anyway

[bold grove]

Yeah, I should

I’ll keep this PIO one for now

[foggy cedar]

For reference, bash would take 27 SECONDS to load when using my ATA PIO driver in old bentobox before I optimized my ext2 driver and wrote an ahci driver

[bold grove]

27 seconds

What

The

Fuck

[foggy cedar]

Yes

Absolute cancer

[radiant grove]

i remember writing my own ata pio driver and used inb's instead of inw's and then wondered why every second byte was a 0

[radiant grove]

[bold grove]

You do use inb in a pio ata driver

You use inw too

loooooong ass macro

#define TURNSTILE_HASH_INDEX(lock_addr) ((((uintptr_t) (lock_addr)) >> 3) & (TURNSTILE_HASH_SIZE - 1))

((((

[radiant grove]

yeah ik

i was supposed to use an inw but i used an inb

[radiant grove]

[bold grove]

Where can I find this driver

Send link

Curious

[radiant grove]

i'd tell you but it's overwritten by team fortress 2 about 49000 years ago

😔

[bold grove]

So yeah, this driver is slow as fuck

[radiant grove]

anyways im gonna write another one later im making a bootloader for the funny

[bold grove]

Like. Extremely. Fucking. Slow.

[radiant grove]

[bold grove]

Look at my new monitor tho guys

[radiant grove]

nice

[radiant grove]

im scared of what it would be like on an actual spinning hard drive

[bold grove]

It would sound like an tornado siren

https://tenor.com/view/sussy-siren-head-uh-oh-gif-25242443

POV my driver:

[radiant grove]

i have a thinkpad with an IDE hard drive it sounds like skeleton bones crackling

its like papyrus lives in there or smth idk

[bold grove]

Nah you just got an ancient Egyptian scribe In your thinkpad

That’s normal

[radiant grove]

lel

[bold grove]

my driver makes my computer heat up 🔥

floppaos comes with free heating and air conditioning

[radiant grove]

depending on whether any file is read

[bold grove]

Making drivers is fun

[radiant grove]

real

[bold grove]

My parents drive me up the wall

Like holy fucking shit

Like

I’m not gonna get any kernel shit done because I’ve had 192728 panic attacks just this fucking morning

[radiant grove]

i thought they broke into your house and sued you for rights for floppaos

"the parts made in our household belong to us, and we did not give you the rights to use them"

[bold grove]

I get my car on Friday!

[radiant grove]

ayy

[simple vault]

Ayy nice

[static tartan]

let's goooo

[bold grove]

I added timeout to my ata driver

Which fixes the freeze upon boot

I just set the timeout to 10000

Whatever

[bold grove]

Happy early new years to everyone!

Imma make a special winter edition of the Flopperating system today!

[radiant grove]

hohoho™

[bold grove]

The Flopperating System, hohoho edition™

[radiant grove]

Flohoho

[bold grove]

New years edition is almost done!

It’s not a kernel change, it just changes the logs and logo and stuff

I just wanted a fun version of FloppaOS for you guys!

[bold grove]

https://github.com/amar454/The-Flopperating-System/releases/tag/v0.1.2

[bold grove]

Happy new years guys! It’s not time for me yet but I wanted to say it anyways now because I’m gonna be drunk as fuck later lol

Cheers to yall

Enjoy the holiday edition

Anyways, I think I’m gonna get to making a text editor

[bold grove]

Idk maybe not

Userspace stuff is kinda boringggg

My kernel has nice name spacing now thankfully

It was so shit before

The only place idc about name spacing is kernel/kernel.c

I could further integrate my init system

Bc technically I still have some initialization before I call my general init() function

Guess I’ll do that

Like my framebuffer init and stuff

Oh shit

I do ata_prepare_op twice…

Well fuck me

Gotta fix that

Dumbass amarat moment

https://tenor.com/view/tryan-trying-blocks-block-head-tryan-blocks-gif-13157134546106029566

Me ^

[bold grove]

finally added all my init stuff to my init function

so my kmain is very simple now

very simple, just like my brain

[bold grove]

God I have this stupid ass fucking issue in my vfs

[violet anchor]

mines simple too!

[foggy cedar]

mine is a bit different, kmain is defined in arch specific code where it initializes the arch specific stuff (incredible right?) and then manually calls generic_startup and then initializes some stuff that requires the vfs (which is initialized by generic_startup) and finally calls generic_main

the random elf64_module call in kmain is for it to load the kernel symbols btw

[bold grove]

Yeah everything for me is generic bc I don’t have a hardware abstraction layer

Don’t plan on having one

Flopperating system is purely 32 bits

Floppa only understands 32 bit

https://tenor.com/view/floppa-big-floppa-lil-floppa-flop-floppa-flop-gif-22883844

[bold grove]

Looks similar to mine

My init() basically does everything

[bold grove]

I use the same theme

[foggy cedar]

i usually use the default theme but it was too dark in broad daylight

with this theme i can read better

[bold grove]

Yeah it’s really nice

Let’s get FloppaOS to 30 stars gang

https://github.com/amar454/The-Flopperating-System

Star it if you haven’t already!!

[radiant grove]

i ate my github account

have a star react

[bold grove]

Thank u

[bold grove]

Did u enjoy your meal

[radiant grove]

it tastes like AI and bad code 😔

specifically like aluminum spaghetti

[bold grove]

Did u vibe code any of your os’s?

[radiant grove]

it depends on if a single itoa function counts as vibe coding

[bold grove]

Everyone vibe codes that shit lmao

[radiant grove]

😭

real

[bold grove]

Waste of time to implement tbh

[radiant grove]

nah i just dont like microsoft

[radiant grove]

real

its useful but like

idk

[bold grove]

All my homies hate Microsoft

[radiant grove]

real

[bold grove]

https://tenor.com/view/denpacc-idiotpack-gif-22042515

[radiant grove]

also i wrote an ATA driver for my bootloader

[bold grove]

Smoking that bill gates pack

[radiant grove]

horribly simple

it only knows like literally one controller

primary master only 😭

[bold grove]

Nice bro

[radiant grove]

good enough for now

[bold grove]

Take a look at my driver

[radiant grove]

mk

[bold grove]

https://github.com/amar454/The-Flopperating-System/blob/main/drivers/ata/ata.c

[radiant grove]

i can send mine (or maybe later when i open source the entire project idk)

[radiant grove]

ight

[bold grove]

Your project isn’t open source??

https://tenor.com/view/wtf-confused-look-gif-24835232

[radiant grove]

uhhh currently

[bold grove]

Open source it then

[radiant grove]

[bold grove]

No reason to keep it closed

No one can help you lol

[radiant grove]

once my bootloader actually does something maybe then

currently it just kind of looks pretty and thats it

[bold grove]

My kernel doesn’t do jack SHIT

But it’s still posted

[radiant grove]

😭

still tho

its too bare bones to post the bare bones version

[bold grove]

fixed the stupid vfs issie

clean

[simple vault]

Mine's pretty simple:

[ivory blade]

your future self is very insulted

[static tartan]

the only thing that interests me is that if () condition

[crimson plover]

why is it interesting

[crimson plover]

meanwhile mine is 800 loc

[torpid viper]

mine is uh something

[paper cloak]

why __assert

[hasty anchor]

Dont question my naming schemes of like 3 years ago

[radiant grove]

[bold grove]

_______init_fart_subsystem

[bold grove]

Rewriting my init system rn

[bold grove]

Well

Maybe not

Idk

This is boring

Init system is a boring ass subsystem

Might work on some drivers

Maybe I should do uacpi

[bold grove]

Idk

Can’t really find anything interesting to work on

I guess I can make a better logging system

[rigid root]

Yes

[radiant grove]

https://cdn.discordapp.com/attachments/1398723862857781440/1453056521696051464/image.gif

[quaint onyx]

https://tenor.com/view/commander-fox-starwars-stupid-droids-fox-clone-wars-gif-21534367

[violet anchor]

alphabetic? ascending?

[bold grove]

I’m having some shrimply krill issues

https://tenor.com/view/krill-issue-gif-4610541527149907170

[bold grove]

Fixing some bugs in my heap allocator rn

I was overwriting my data structure which I keep within each box

Boxes are just pages divided into 32 byte blocks

And I place the box info then after that the bitmap, then the actual blocks themselves

So [info][bitmap][block 1][block 2] etc etc

[bold grove]

rehauled the heap allocator

[static tartan]

are u making this in assembly (i assume)?

[crimson plover]

he is not

what gives u that impression

[static tartan]

oh im a dumbass
i didnt even look at the repo

mb

[bold grove]

Why would I make an os in assembly

[radiant grove]

because its funny

[bold grove]

Funny waste of time

[bold grove]

It’s ok lol

[static tartan]

thx lol
but trust me assembly is based af if you use AVX2/AVX512
also fasm lets u make assembly -> executable app
for linux, windows and others

[bold grove]

Any assembler lets you makes executable application…

[static tartan]

oh
well im stupid ig

[bold grove]

What else would an assembler do?

Besides making executables

[bold grove]

Rehauled the early allocator

[paper cloak]

C intrinsics do this

[bold grove]

Beer for lunch today

[azure rapids]

That sounds like fucking torture

[paper cloak]

its a bit of a weird statement because you can totally use SIMD intrinsics in C

albeit not with as much control over registers

[azure rapids]

Yeah that’s what I was thinking why not just use intrinsics

[paper cloak]

and you can have free "portability" using things like sse2neon

[azure rapids]

Iirc you can use some syntax to force gcc/clang to put a variable into a specific register

If that works for sse/avx regs idk

[paper cloak]

probably

but there are better more portable ways to indicate vectorization too

using #pragma omp simd

[bold grove]

Yeah there’s a register keyword

[azure rapids]

Yeah I just don’t know if that works for sse/avx regs

[bold grove]

It doesn’t iirc

I think it’s just gprs

I’m actually pretty proud of this heap allocator I made

It’s like the only unique thing I’ve done

Dude I made so much money today

Fucking amarat is stacked

[static tartan]

it is but i love it
i can sum N (where N is a power of two) numbers in O(log2(N)) time

[azure rapids]

Hm send it somewhere

Prob not here

I’m interested

[static tartan]

it's just movaps, shufps and vaddps
not much to see there

but if u still want it incase u wanna sum 16 floats together
i can give it to ya

(warning: avx2 required)

[bold grove]

It’s ok if he sends it here

[azure rapids]

Oh okay

[bold grove]

Flopperating system thread is our thread

[static tartan]

da

[bold grove]

https://tenor.com/view/wave-gif-11960435592549008198

[static tartan]

do u need to sum up 16 floats tho

[azure rapids]

nah I'm just curious what it looks like

[bold grove]

Proleteri svih zemalja, ujedinite se!

https://tenor.com/view/comunisto-dogo-gif-15433861177915232836

Yall just radicalized me

[static tartan]

    vmovaps ymm0, [floats1]
    vmovaps ymm1, [floats2]

    ; --- Fast summation algorithm - Time O(log2(n)) ---

    ; halved once
    vaddps ymm0, ymm0, ymm1

    ; halved twice
    vextractf128 xmm0, ymm0, 0
    vextractf128 xmm1, ymm0, 1

    vaddps xmm0, xmm0, xmm1

    ; halved thrice
    movaps xmm1, xmm0
    shufps xmm1, xmm0, 0xee

    vaddps xmm0, xmm0, xmm1

    ; halved 4x (final result)
    movaps xmm1, xmm0
    shufps xmm1, xmm0, 0x11

    vaddps xmm0, xmm0, xmm1

    vcvttss2si eax, xmm0 ; this is just the "extract result" step

i am madlad 🔥

[azure rapids]

oh wtf

that's sick

[static tartan]

log2(16 floats) = 4
i halve 4 times
checks out

[bold grove]

Nice

Cool stuff

[static tartan]

if you have enough space, you can sum up any amount of floats where N is a power of 2, but efficiency will decrease

though registers are preferred

[bold grove]

Do u speak a slavic language

[azure rapids]

I was TRYING to get clang to emit something like that

but guess what

[static tartan]

but uhh i think u need to have 64 bit

[bold grove]

Clang sucks ass

[static tartan]

ano 👍

[bold grove]

Gcc better

[azure rapids]

It decided to just constant fold the whole thing

[bold grove]

Czech?

[static tartan]

so close yet so far
🇸🇰 Slovak

[bold grove]

Ahoj motherfucker

[simple vault]

Ye

[bold grove]

I’m bosnian 🇧🇦

You just triggered so many Slovaks

💀

Serbia is fucked

[azure rapids]

well okay

that's one way to codegen it

[static tartan]

and could u pls delete this one

[gray cairn]

https://tenor.com/view/baby-laugh-ai-baby-babyfryingme-baby-sob-folk-gif-18221933230434867320

[static tartan]

wait do u measure in uops or uflops

[static tartan]

bro wha

[gray cairn]

random

[bold grove]

Uflops

[ivory blade]

omg i just learned gcc is not gnu c compiler

[cobalt nebula]

Used to be

[paper cloak]

Using AVX that literally takes like two operations tho

[static tartan]

i made it better by using vhaddps btw

[static tartan]

[bold grove]

Gcc isn’t just a c compiler

It does like everything

[ivory blade]

gnu compiler collection

[bold grove]

Ye

[bold grove]

Life is an uphill battle. Appreciate what you have. One day it might be taken away from you. In this world there is very little good and lots of bad. Appreciate the good that you have and appreciate the opportunities you have to succeed and take them. Stay in school. Stay off drugs. This is coming from the biggest addict ever. Don’t break laws, don’t get in trouble, don’t get in fights. These are trivial mistakes that have impacted my life. I have a criminal record due to my recklessness. Please stay safe and strong. Sorry for the rant. Have a good day guys and please, again, appreciate what you have.

Drugs are the main issue. Please stay off them. Your sober life is much more valuable than a high one.

Please listen to me when it comes to this, and other stupid mistakes. I got a criminal record from vandalism and getting in fights at school. Don’t make these trivial mistakes. At this point I’ve lost everything.

[timber terrace]

your doing well with how well your holding up mate, genuinely you should be proud of yourself - you've made mistakes but any other person i know would've succumbed by now - you'll find your way out of this somehow

[quaint onyx]

Paragraphs?

Nvm that's 16 bytes.

[bold grove]

I feel mentally better today.

There will be progress on the os, sorry it’s been like 3 days since I’ve updated the repo

Cool stuff coming though

Stay tuned

[bold grove]

Dang it’s been 5 days since my last commit

I’m just gonna commit what I have

[rigid root]

ultra with literal months since last commit ☠️

[radiant grove]

kvass with NO commit ☠️☠️

[bold grove]

Im in the hospital now

Sorry guys.

I’ll update you guys when I’m better

I haven’t had me medication for several days

So good night

[radiant grove]

WHAT HAPPENED

[bold grove]

Too much

[azure rapids]

Aw :( hope you get better

[radiant grove]

insanity

sad tho

good luck

[ivory blade]

why didnt discord scroll wtf

sry

[ivory blade]

hope you get better

[bold grove]

Ok I got discharged

I had some mental episodes

[ivory blade]

stay hard

[bold grove]

I’m good guys :)

[azure rapids]

Yay 🥳

[static tartan]

[coarse root]

nice!

[bold grove]

there seems to be an issue within my vfs again

not quite sure what

ive been kinda lazy on the os

school started so ive been busy asf

[bold grove]

might be taking a slight break

i say that but theres still a 20% chance i drop something new today

theres a bug in my vfs i cannot figure out

gdb is not helping

im page faulting when mounting

which makes no damn sense

it happens within my tmpfs_init()

[bold grove]

I’m thinking about making my physical allocator a free list

I know that a buddy system is basically a free list but

[bold grove]

I wanna make a kernel that is a NT larp

I don’t think I’m skilled enough for that tho

The Flopperating system barely works half the time

Reliability

I need better rng within my kernel

My rng is bullshit

I think imma base it off my time_get_current integer

And just create a random number based off that

[bold grove]

The second I say this I got hella motivation

I’m gonna actually document some shit today maybe

Recently I’ve been doing less new implementations… just been fixing my old ones

Like for example I made my framebuffer thing alot better

I need to make a dev fs

Still have get to get to that

I made my ata driver better too

Added a proper timeout

Previously it took like 40 seconds to boot Because of all the busy waiting

[bold grove]

Man I’m doing some testing and Flopperating system is slow 😖

[radiant grove]

:(

[bold grove]

This song is so good

This too

[radiant grove]

nice

[bold grove]

If yall listen to the lyrics of took her to the o you’ll know what my life is

Honestly I live a pretty ratchet life

Not even a flex

Life is hard

[bold grove]

My physical allocator is quick as FUCK though

Like my pmm

It benchmarked very well

And I looked at the disassembly and it was pretty efficient

So I won’t be changing my pmm

Because a simple free list will be slower

[bold grove]

Well idk

Will a FIFO free list be faster or slower than a buddy system

Does anyone know

Idk how to test it without making a new ass allocator

[bold grove]

Ive been doing so much yapping in here and like no work on the os

Imma redo my GDT (least relevant thing ever)

[bold grove]

Decided this was a dumb idea

[radiant grove]

nono

you WILL, yes, WILL rewrite the gdt

its a part of memory management crap too

[bold grove]

i got jumpscared by floppa

[radiant grove]

fleppa

[simple vault]

Damn

Imagine coding really late at night and having that show up.

[bold grove]

Fucking scary

Documented my interrupts

[violet anchor]

use ansi to make floppas eyes red

[bold grove]

Evil floppa

[static tartan]

make bad apple

[bold grove]

Sorry I’ve been wasting my time these past couple days doing stupid childish shit

[radiant grove]

if anything, osdev is a waste

do whatever you want man we dont care

[simple vault]

As long as you do stuff that makes you happy and that doesn't hurt yourself we'll all be happy

[bold grove]

Yeah. I honestly agree with this atm

I’m at a plateau

Don’t know what I can implement that will be fun anymore

The ata driver was fucking lit

[radiant grove]

uhh file system

idk its the next logical thing

file system then programs and crap

[bold grove]

I need to rewrite my file system entirely

Vfs is ok

Tmpfs is not it tho

[radiant grove]

the hard drive one

[bold grove]

File system ≠ ata driver

[bold grove]

I don’t want people to lose interest in my project tho :’(

I feel like if I don’t post enough people will stop looking

[rigid root]

we're always here

[bold grove]

yay thank you infy

guess what guys

keyboard driver

my old one is outdated

so im making a new one

and re adding it

because for a long time it didngt work with my new kernel api

i made the keyboard driver way in the beginning

[radiant grove]

PLAYSTATION/2

[bold grove]

Made a keyboard data structure

With a normal and shift key map

Each keyboard_t struct has a keyboard_layout_t enum in it

So I can easily make many layouts

I have an interesting idea

Making each subsystem have its own binary

So each is a loaded elf file

Running as a process

Like a userspace process

Maybe I just redescribed fucking microkernels god damn it

[torpid viper]

so basicly tou want to make a microkernel ?

you can mix what you have currently with thay if you want

to get a hybrid

like for exemple driver in userspace but vfs in kernel spacz

[bold grove]

Yeah but the hybrid term is kinda dumb

[bold grove]

Gonna switch to @crimson plover ‘s build system, fabricate

Shout out to him

[radiant grove]

shout out to you random person

[azure rapids]

ayy

if only it worked on macos 😭

[languid talon]

Fab kinda goated ngl

[bold grove]

not random person

[radiant grove]

shout out to you not random person

[crimson plover]

bro it should but u wont help me fix it and I dont have a macbook 😭

[bold grove]

fabricate works!

[radiant grove]

certified unix, they said

[azure rapids]

I have no idea what the problem is lmao

I don't do lua

when I get home in [today but in like 7 hours] I'll fix it

[bold grove]

keyboard driver added!

made a cute data structure for it

[bold grove]

I’m not gonna use the keyboard for now

I’m not even close to a good userspace

I should start porting software

I have all the syscalls to implement bash

[azure rapids]

the chariot ecosystem must grow

[simple vault]

Just need to port a stdlib then

[bold grove]

I made my pio ata driver better and faster

Also thank u guys for your continued interest and support towards my project. I really appreciate all of you and it makes me happy.

OSdev is actually one of the few things that makes me happy

Anyways. It might be smp time

I need to figure out AP startup

Thankfully I have synchronization primitives so my whole kernel api is thread safe

Also I might make my kernel modular soon

I’ve been reading lots of FreeBSD code

Which is ironically used by the iPhone I’m on rn

Darwin ftw

Ok I decided what I’m gonna work on

New vmm

The api will stay the same

At least the core api

It’s too much work to to keep aslr so I’m removing that. It’s basically a useless feature

Also I might work on making my heap allocator even faster

[radiant grove]

based

[radiant grove]

OHNO MULTIPROCESSING

[bold grove]

Yeeee

I made a nice syscall dispatch macro too

[radiant grove]

nice

[bold grove]

Imma make a new todo list

Let’s see if I get any of these goals done tonight

I think fixing the box allocator is doable

[ivory blade]

ahh everyone has multitasking except me

[bold grove]

It’s not super hard

[bold grove]

well i got nothing done

Spent too much time documenting

I’m making all the source files have a description at the top after license

[static tartan]

🍎 🥀

[bold grove]

No work so far

Might work on the heap

[bold grove]

I promise I’ll work on the kernel tonight it’ll just be later at night

Probably some more documentation work and some kernel internal stuff

Particularly the allocator

[bold grove]

I really wish i could explain why this is so funny but I can’t

This is fucking hilarious

The joke is that those are the three rotating presidents (yes, that’s not a joke) and all of their names say shit like “seik the cheater” “seik that’s fucking us” and “seik that will destroy us” but it’s stylized as Arabic names😭😭

[radiant grove]

this is funny even without understanding what it says

peak meme

[ivory blade]

its a meme from 2027, you wont understand

[bold grove]

True statement

[bold grove]

Working on the kernel rn

First time in a bit that I’ve sat down and worked on it

I usually do it for short periods of time but now I’m locked in

Redbull at 9pm

Most locked OSdev

[radiant grove]

insane

[azure rapids]

yay

[ivory blade]

ew kernel shell

[bold grove]

That was before I knew how cringe that was

But that shell was in userspace

I had a cursed ass userspace entry function

[ivory blade]

oh

otos is my first project with userspace

other 3 times it was kernel shell with giving programs a struct with function adresses

[final wyvern]

can't wait for tf2os

[bold grove]

Lmao

Real

My os is team fortress os

[bold grove]

i think its time for smp guys

rewriting scheduler

[azure rapids]

:O

[bold grove]

doing mmio tho

bc i didnt have that

LETS GOOO

[rigid root]

u really want inline asm for this

first of all u want to use EAX, you also want the compiler to not attempt to change the width of the store, which it may do

[bold grove]

Ok bet

Thank u

I kinda realize now that the compiler has the discretion to do that

I’ll fix this now

[radiant grove]

medieval torture

[azure rapids]

oof

now I gotta fix it too

[bold grove]

FUCK YOU

[radiant grove]

https://tenor.com/view/soviet-union-stalin-gif-25176129

off to gulag you go for insulting the highest power

[bold grove]

Anyways

Apic driver in the works

I already did the trampoline

So the protected mode jump is done

Now I just need a routine to actually call my trampoline

Then I need an ap start up function

Which will be called by the trampoline after the task register and shit is loaded

Just wish life didn’t get in the way as much because I would have a much better kernel

I never had a name for my kernel but I think I’ll just name the TFSK

(The Flopperating system kernel)

[radiant grove]

the f***ing system kernel

[bold grove]

I might get smp done by tonight or tmr

[bold grove]

Done studying for school

Lock in time

Wish me luck gang

[azure rapids]

good luck!

[bold grove]

I’m almost done with smp

Haven’t tested anything tho

[radiant grove]

so you ain't

test it and get funny printf bugs

[bold grove]

My printf implementation might be some of the most horrendous shit I’ve ever made

My str.h is a straight 1000 lines of pain

[radiant grove]

i need to make my own printf

just for experience

except like

no floats

[radiant grove]

insanity

https://cdn.discordapp.com/attachments/1305395406662012928/1461085614194688050/speechmemified_image-8.gif.gif

[bold grove]

DIE

DONT BRING THAT UP EVER

[radiant grove]

"thy end is now"

[radiant grove]

https://tenor.com/view/rukocord-gif-19005042

[bold grove]

You’re banned from the crusty crab for bringing up my attempted mmio

[radiant grove]

secret formula (the real contents of void fuckshit())

[radiant grove]

krusty krab knockoff 😔

[bold grove]

void fuckshit() lore goes hard

In nyaux we trust

[radiant grove]

IT CAME FROM NYAUX?!?!?!?!?

[bold grove]

Ofc

This was before you were in the server

I think

I thonk

[radiant grove]

i think i joined in nyaux's last days

before the dude left

[bold grove]

He didn’t leave

He got banned

[radiant grove]

banned

i wonder if he's coming back though

or they

whoever

[bold grove]

Idk they had many chances

[bold grove]

The whole staff got fed up bc he has some mental issues

[radiant grove]

oh

[bold grove]

I’m no stranger for mental illness either tho

Amarat lore goes insane

[radiant grove]

im no stranger to people getting fed up with me

happens sometimes lel

[radiant grove]

do be true

amarat video essay (3:38:34 long)

[bold grove]

I wish I was here for the real bad parts of my life lol

I was here when I was homeless

OSdev: veteran difficultly

OSdev with no wifi went crazy

[radiant grove]

insanity

i mean ive had some unjust bullcrap in life as well i empathize 😔

[bold grove]

Life sucks man

OSdev brings me joy tho

[radiant grove]

nah mostly america

[radiant grove]

same

[bold grove]

I shoved my entire apic driver into interrupts.c

[radiant grove]

WHAT

oh nvm

[bold grove]

I meant apic

[radiant grove]

it said ata for a moment

ata dma can not be this good to deplete even the budget for making .c files /j

[bold grove]

I don’t even have dma

I just have a pio driver

[radiant grove]

relatable

[bold grove]

But I did some things to make it decently fast

[radiant grove]

fair

honestly make a dma driver when you can

speed™

[bold grove]

I need dma in general

[radiant grove]

true

sata when

floata

does floppaos have any ported software actually

[bold grove]

No idc to port anything

I don’t even have a proper libc

Only my own lib

Floplib ™

[radiant grove]

are you gonna make your own software

[bold grove]

Yes

[radiant grove]

fartslibC--

[radiant grove]

based

(same)

there better be a floppaos sdk

you have 3 days, i'm gonna go assemble the mafia

[bold grove]

Yeah there will be

[radiant grove]

yay

[bold grove]

Me with gang connections:

Jk

[radiant grove]

gang vs mafia

bowser vs eggman type crap

[bold grove]

“Took her to the o” by king von

[radiant grove]

a

[bold grove]

My ass is tryna stay out of crime and I listen to music that does nothing but talk about crimes 🔥

Abg by quando rondo is fire too

[radiant grove]

many people here listen to love songs but i dont think they get any dont worry

[bold grove]

Real 😞

[radiant grove]

time to add this song into "the temporary brain contents (wiped every time i sleep)"

[bold grove]

Yes

[radiant grove]

real

[bold grove]

https://youtu.be/CaW5JW8NXRo?si=-Tw2s3TcTmelHTn5

Straight heat

[radiant grove]

good song i guess (im a metalhead 😔)

[bold grove]

ironically my smp scheduler is just 300 lines