diff options
| author | Arthur Hanson Rasmusson <arthur@vgpu.io> | 2026-10-07 14:59:19 -0400 |
|---|---|---|
| committer | Arthur Hanson Rasmusson <arthur@vgpu.io> | 2026-10-07 14:59:19 -0400 |
| commit | cf65fc4ba9011e2214dc00e198599e581fc391ee (patch) | |
| tree | 6b76831ff0892383080deae6204088ba53370832 /kernel/irq.c | |
| parent | 6e6647c779708ab1a206c69ea31bdce97df22b8e (diff) | |
| download | open-iov-cf65fc4ba9011e2214dc00e198599e581fc391ee.tar.gz open-iov-cf65fc4ba9011e2214dc00e198599e581fc391ee.zip | |
vgsp: m104 - inject the mail_kernel module-data base when bank-4 is empty
The forwarded mail_kernel reads __device__ kMail through c[0x4][0x0] (the
driver-provided module-data base), but the guest's bank-4 page content is
zero in the launch (the driver's value never lands in the resolved page).
With gr_mail_patch set, when bank 4's first 8 bytes are zero, allocate a
module page holding the demo message, map it at server-managed VA
0x11ff00000 (UPDATE_PDE_2, inside [0x100000000,0x11fffffff)) and point
c[0x4][0x0] there. The kernel then reads the message from device memory and
writes out[i] through the already-relocated bank-0 pointer; vadd (params
only) becomes the real relocated-data acceptance test.
Diffstat (limited to 'kernel/irq.c')
0 files changed, 0 insertions, 0 deletions
