hal/metal/tests.lisp
in-package#:luvcraft.tests
deftestslug-formats-have-exact-portable-and-metal-storage
ok
=4
texture-format-bytes-per-texel:rg16-uint
ok
ok
ok
=metal:+pixel-format-rg16-uint+
luv::metal-resource-pixel-format:rg16-uint
make-texture-descriptor:format:rg16-uint
ok
=metal:+pixel-format-rg16-float+
luv::metal-resource-pixel-format:rg16-float
make-texture-descriptor:format:rg16-float
ok
=metal:+pixel-format-rgba16-float+
luv::metal-resource-pixel-format:rgba16-float
make-texture-descriptor:format:rgba16-float
deftestmetal-slug-textures-accept-their-exact-packed-words
let*
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
band-texturenil
curve-texturenil
unwind-protect
progn
setfband-texture
createdevice
curve-texturemake-texture-descriptor:size'
21
:dimensions:2d:format:rg16-uint:usage':texture-binding:copy-dst
createdevice
make-texture-descriptor:size'
21
:dimensions:2d:format:rgba16-float:usage':texture-binding:copy-dst
ok
equal'
211
gpu-texture-sizeband-texture
ok
equal'
211
gpu-texture-sizecurve-texture
write-texturequeue
make-texture-copy:textureband-texture
make-array'
12
:element-type'unsigned-byte32
:initial-contents'#x00020001#x00040003
make-texture-data-layout:bytes-per-row8:rows-per-image1
'21
write-texturequeue
make-texture-copy:texturecurve-texture
make-array'
12
:element-type'unsigned-byte64
:initial-contents'#x3c00380034003000#x40003c0038003400
make-texture-data-layout:bytes-per-row16:rows-per-image1
'21
ok
ok
let
unexpectednil
unwind-protect
progn
setfunexpected
ok
ok
member:storage-binding
gpu-texture-usageunexpected
whenunexpected
destroyunexpected
whencurve-texture
destroycurve-texture
whenband-texture
destroyband-texture
destroydevice
deftestadopted-metal-textures-enter-explicit-residency
let*
device
request-gpu-device
make-instance'metal-gpu-provider
nativenil
texturenil
unwind-protect
progn
setfnative
metal:new-metal-texture
luv::metal-native-objectdevice
88metal::+pixel-format-r8-unorm+metal:+texture-usage-shader-read+:storage-modemetal:+storage-mode-private+:label"adopted residency probe"let
setftexture
adopt-native-texturedevicenativeowner
make-texture-descriptor:size'
88
:dimensions:2d:format:r8-unorm:usage':texture-binding
ok
luv::metal-texture-resident-ptexture
ok
equal'
881
gpu-texture-sizetexture
ok
not
luv::metal-texture-owned-ptexture
destroytexture
setftexturenil
ok
not
objc:objective-c-object-released-pnative
whentexture
destroytexture
whennative
destroydevice
deftestmetal-coalesces-multiple-sampled-texture-preparations
let*
device
request-gpu-device
make-instance'metal-gpu-provider
encodernil
colornil
depthnil
unwind-protect
progn
setfencodercolor
createdevice
depthmake-texture-descriptor:size'
88
:dimensions:2d:format:rgba8-unorm:usage':render-attachment:texture-binding
createdevice
make-texture-descriptor:size'
88
:dimensions:2d:format:depth32-float:usage':render-attachment:texture-binding
ok
luv::metal-encoder-pending-consumer-barrierencoder
ok
gethashcolor
luv::metal-encoder-resourcesencoder
ok
gethashdepth
luv::metal-encoder-resourcesencoder
whenencoder
destroyencoder
whendepth
destroydepth
whencolor
destroycolor
destroydevice
deftestmetal-chained-blits-observe-the-prior-blit-write
let*
width641
height359
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
sourcenil
intermediatenil
readbacknil
encodernil
command-buffernil
unwind-protect
progn
setfsourceintermediatereadbackencoder
end-pass
begin-render-passencoder
make-render-pass-descriptor:color-attachments`
:view,source:load-op:clear:store-op:store:clear-value
1.00.01.01.0
setfcommand-buffer
finishencoder
whencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
whenreadback
destroyreadback
whenintermediate
destroyintermediate
whensource
destroysource
destroydevice
deftestworld-text-cache-reuses-shaping-and-device-glyphs
let*
device
request-gpu-device
make-instance'metal-gpu-provider
cache
font
cl-dejavu:font-pathname"DejaVuSans.ttf"
camera
make-instance'fly-camera
firstnil
secondnil
unwind-protect
progn
let
first-glyphs
luvcraft::world-text-run-glyphsfirst
second-glyphs
luvcraft::world-text-run-glyphssecond
resources-by-glyph
make-hash-table
saw-repeated-glyph-pnil
ok
ok
ok
ok
ok
dolist
glyphfirst-glyphs
let
glyph-id
luv.slug:slug-glyph-placement-glyph-idglyph
multiple-value-bind
resourcepresent-p
gethashglyph-idresources-by-glyph
ifpresent-p
progn
setfsaw-repeated-glyph-pt
ok
eqresource
luv.slug:slug-glyph-placement-resourceglyph
setf
gethashglyph-idresources-by-glyph
luv.slug:slug-glyph-placement-resourceglyph
oksaw-repeated-glyph-p
loopforfirst-glyphinfirst-glyphsforsecond-glyphinsecond-glyphsdo
ok
eq
luv.slug:slug-glyph-placement-resourcefirst-glyph
luv.slug:slug-glyph-placement-resourcesecond-glyph
whenfirst
destroydevice
objc:define-objective-c-messagemake-test-metal-layer
"new":object:ownership:owned:class"CAMetalLayer"
defuninstall-metal-live-probe-vertex
eval'
luv.shader:define-shader-methodluv.shader:shader-specification-formetal-live-probe-vertex-specification
role
eql:metal-live-probe
stage
eql:vertex
let*
clip
luv.shader:set-outputclip-positionclip
defuninstall-metal-live-probe-fragment
red&keyinvalid-p
eval`
luv.shader:define-shader-methodluv.shader:shader-specification-formetal-live-probe-fragment-specification
role
eql:metal-live-probe
stage
eql:fragment
:stage,
ifinvalid-p:compute:fragment
:outputscolor:vec4:location0
let*
deftestmetal-messages-retain-structure-abi
let
ok
equal
getfsize:selector
"setDrawableSize:"ok
ok
equal
getfclear:selector
"setClearColor:"ok
ok
equal
getfargument-buffer:selector
"setAddress:attributeStride:atIndex:"ok
ok
equal"drawIndexedPrimitives:indexCount:indexType:indexBuffer:indexBufferLength:instanceCount:baseVertex:baseInstance:"
ok
equal
getfdraw-mesh:selector
"drawMeshThreadgroups:threadsPerObjectThreadgroup:threadsPerMeshThreadgroup:"ok
deftestcanvas-presentation-policy-is-explicit-and-provider-specific
ok
equal'
:vulkan:resizable:hidden
ok
ok
eq:vulkan
luv::sdl-presentation-api-for
make-instance'vulkan-gpu-provider
ok
eq:metal
luv::sdl-presentation-api-for
make-instance'metal-gpu-provider
let
canvas
make-sdl-canvas:presentation-api:vulkan
ok
deftestnative-close-can-be-deferred-for-application-teardown
let
timestampsnil
setf
lambda
native-canvasevent
declare
ignorenative-canvas
push
:defer-canvas-closecanvas-event-timestampevent
timestampsThis is the SDL event macOS emits for Command-Q, distinct from clicking one window's close button.
cffi:with-foreign-object
event'
:structsdl3:common-event
setf
cffi:foreign-slot-valueevent'
17:structsdl3:common-event
'sdl3::%timestampok
equal'
170
timestampssetfnil
ok
luv::sdl-canvas-close-requested-pcanvas
deftestmetal-provider-owns-a-real-metal-4-queue
let
device
request-gpu-device
make-instance'metal-gpu-provider
unwind-protect
progn
ok
ok
ok
equal
objc:objective-c-object-protocol-name
"MTL4CommandQueue"luv::metal-native-object
device-queuedevice
ok
equal
objc:objective-c-object-protocol-name
"MTLResidencySet"luv::metal-device-residency-setdevice
ok
equal
objc:objective-c-object-protocol-name
"MTLSharedEvent"luv::metal-queue-completion-event
device-queuedevice
destroydevice
deftestmetal-device-owns-a-real-metal-4-compiler
let
device
request-gpu-device
make-instance'metal-gpu-provider
unwind-protect
ok
equal
objc:objective-c-object-protocol-name
"MTL4Compiler"metal-device-compilerdevice
destroydevice
deftestluvcraft-shader-compiles-in-memory-on-the-metal-device
let
specification
device
request-gpu-device
make-instance'metal-gpu-provider
modulenil
unwind-protect
progn
setfmodule
createdevice
make-shader-module-descriptor:label"block fragment Metal library":language:mathematical:codespecification
ok
ok
eqspecification
luv.msl:msl-document-specification
metal-shader-module-documentmodule
ok
string=
metal-shader-module-entry-pointmodule
"block_world_fragment_specification"ok
ok
equal
objc:objective-c-object-protocol-name
"MTLLibrary"luv::metal-native-objectmodule
whenmodule
destroymodule
destroydevice
deftestluvcraft-vertex-and-fragment-link-as-a-metal-4-render-pipeline
let
device
request-gpu-device
make-instance'metal-gpu-provider
vertex-modulenil
fragment-modulenil
pipelinenil
unwind-protect
progn
setfvertex-module
createdevice
fragment-modulemake-shader-module-descriptor:label"block vertex Metal library":language:mathematical:code
createdevice
pipelinemake-shader-module-descriptor:label"block fragment Metal library":language:mathematical:code
createdevice
make-render-pipeline-descriptor:label"block world Metal 4 pipeline":layoutnil:vertex`
:module,vertex-module:buffers
:fragment`:array-stride64:attributes
:shader-location0:offset0:format:float32x3
:shader-location1:offset12:format:float32x3
:shader-location2:offset24:format:float32x3
:shader-location3:offset36:format:float32x3
:shader-location4:offset48:format:float32x4
:module,fragment-module:targets
:primitive':format:bgra8-unorm:blend:premultiplied-alpha
:topology:triangle-list
:depth-stencil':format:depth32-float:depth-write-enabledt:depth-compare:less
ok
ok
equal
objc:objective-c-object-protocol-name
"MTLRenderPipelineState"luv::metal-native-objectpipeline
ok
equal
objc:objective-c-object-protocol-name
"MTLDepthStencilState"metal-render-pipeline-depth-stencil-statepipeline
whenpipeline
destroypipeline
whenfragment-module
destroyfragment-module
whenvertex-module
destroyvertex-module
destroydevice
deftesttask-mesh-pipeline-carries-uint64-and-draws-on-metal-4
let
device
request-gpu-device
make-instance'metal-gpu-provider
task-modulenil
mesh-modulenil
fragment-modulenil
pipelinenil
targetnil
readbacknil
encodernil
command-buffernil
unwind-protect
progn
setftask-module
createdevice
mesh-modulemake-shader-module-descriptor:label"task uint64 Metal library":language:mathematical:code
createdevice
fragment-modulemake-shader-module-descriptor:label"mesh uint64 Metal library":language:mathematical:code
createdevice
pipelinemake-shader-module-descriptor:label"mesh fragment Metal library":language:mathematical:code
createdevice
targetmake-mesh-render-pipeline-descriptor:label"task mesh uint64 Metal 4 pipeline":layoutnil:task`
:module,task-module
:mesh`:module,mesh-module
:fragment`:module,fragment-module:targets
:max-mesh-workgroups1:format:rgba8-unorm
createdevice
readbackencodermake-texture-descriptor:label"task mesh proof target":size'
3232
:dimensions:2d:format:rgba8-unorm:usage':render-attachment:copy-src
ok
ok
ok
let
pass
begin-render-passencoder
make-render-pass-descriptor:color-attachments`
:view,target:load-op:clear:store-op:store:clear-value
0.00.00.01.0
end-passpass
setfcommand-buffer
finishencoder
let
pixels
read-bufferreadback
ok
whencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
whenreadback
destroyreadback
whentarget
destroytarget
whenpipeline
destroypipeline
whenfragment-module
destroyfragment-module
whenmesh-module
destroymesh-module
whentask-module
destroytask-module
destroydevice
deftestfailed-metal-library-keeps-the-device-compiler-usable
let*
device
request-gpu-device
make-instance'metal-gpu-provider
specification
bad-document
luv.msl:compile-mslspecification
modulenil
failurenil
setf
luv.msl:msl-document-sourcebad-document
"this is deliberately not Metal source"unwind-protect
progn
handler-case
luv::metal-gpu-error
condition
setffailurecondition
okfailure
ok
eq
luv::metal-gpu-error-reasonfailure
:library-compilation-failedok
stringp
getf
luv::metal-gpu-error-detailsfailure
:diagnosticsetfmodule
ok
whenmodule
destroymodule
destroydevice
deftestlive-metal-pipeline-retains-last-good-and-recovers
let
device
request-gpu-device
make-instance'metal-gpu-provider
artifactnil
unwind-protect
progn
setfartifact
luvcraft::make-live-shader-pipeline:role:metal-live-probe:vertex-role:metal-live-probe:label"live Metal pipeline probe":devicedevice:layoutnil:vertex-buffers':target-format:bgra8-unorm:primitive'
:array-stride12:attributes
:shader-location0:offset0:format:float32x3
:topology:triangle-list
:depth-stencilnillet
first-pipeline
luvcraft::live-shader-pipeline-native-pipelineartifact
ok
ok
eq:installed
live-shader-pipeline-statusartifact
ok
eq:failed
live-shader-pipeline-statusartifact
ok
eqfirst-pipeline
luvcraft::live-shader-pipeline-native-pipelineartifact
ok
not
luv::metal-object-destroyed-pfirst-pipeline
let
replacement
luvcraft::live-shader-pipeline-native-pipelineartifact
ok
eq:installed
live-shader-pipeline-statusartifact
ok
ok
not
eqfirst-pipelinereplacement
ok
luv::metal-object-destroyed-pfirst-pipeline
ok
whenartifact
destroydevice
deftestlive-metal-pipeline-replacement-retires-after-its-in-flight-draw
let*
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
artifactnil
texturenil
verticesnil
encodernil
commandsnil
old-native-pipelinenil
unwind-protect
progn
setfartifact
luvcraft::make-live-shader-pipeline:role:metal-live-probe:vertex-role:metal-live-probe:label"in-flight Metal pipeline probe":devicedevice:layoutnil:vertex-buffers':target-format:bgra8-unorm:primitive'
texture:array-stride12:attributes
:shader-location0:offset0:format:float32x3
:topology:triangle-list
:depth-stencilnilcreatedevice
verticesmake-texture-descriptor:label"in-flight pipeline target":size'
1616
:dimensions:2d:format:bgra8-unorm:usage':render-attachment
write-buffervertices
make-array9:element-type'single-float:initial-contents'
-0.7-0.60.00.7-0.60.00.00.70.0
let
old-pipeline
luvcraft::live-shader-pipeline-native-pipelineartifact
setfold-native-pipeline
luv::metal-native-objectold-pipeline
encoderlet
pass
begin-render-passencoder
make-render-pass-descriptor:color-attachments
list
list:viewtexture:load-op:clear:store-op:store:clear-value
0.00.00.01.0
end-passpass
setfcommands
finishencoder
ok
luv::metal-object-destroyed-pold-pipeline
ok
not
eqold-pipeline
luvcraft::live-shader-pipeline-native-pipelineartifact
submitted-work-donequeue
ok
objc:objective-c-object-released-pold-native-pipeline
whencommands
destroycommands
whenencoder
destroyencoder
whenvertices
destroyvertices
whentexture
destroytexture
whenartifact
destroydevice
deftestmetal-buffer-populates-a-native-metal-4-argument-table
let
device
request-gpu-device
make-instance'metal-gpu-provider
buffernil
argument-tablenil
unwind-protect
progn
setfbuffer
write-bufferbuffer
make-array9:element-type'single-float:initial-contents'
-0.65-0.550.00.65-0.550.00.00.700.0
multiple-value-bind
tablediagnostic
metal:new-metal-4-argument-table
luv::metal-native-objectdevice
1:label"argument table probe":attribute-strides-ptok
nulldiagnostic
setfargument-tabletable
metal:set-metal-argument-table-bufferargument-table
metal:metal-buffer-gpu-address
120luv::metal-native-objectbuffer
ok
ok
plusp
metal:metal-buffer-gpu-address
luv::metal-native-objectbuffer
ok
equal
objc:objective-c-object-protocol-nameargument-table
"MTL4ArgumentTable"ok
whenargument-table
objc:release-objective-c-objectargument-table
whenbuffer
destroybuffer
destroydevice
deftestmetal-finish-produces-one-shot-portable-work-with-dependencies
let*
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
texturenil
encodernil
command-buffernil
native-texturenil
native-command-buffernil
allocatornil
unwind-protect
progn
setftexture
createdevice
native-texturemake-texture-descriptor:label"portable Metal work dependency":size'
88
:dimensions:2d:format:rgba8-unorm:usage':render-attachment
luv::metal-native-objecttexture
encodersetfcommand-buffer
finishencoder
native-command-bufferluv::metal-native-objectcommand-buffer
allocatorluv::metal-command-buffer-allocatorcommand-buffer
ok
ok
ok
membertexture
luv::metal-command-buffer-resourcescommand-buffer
ok
eq:submitted
luv::metal-command-buffer-statecommand-buffer
ok
ok
Logical invalidation is immediate. Native retirement follows the
shared-event completion frontier without blocking destroy.
destroycommand-buffer
setfcommand-buffernil
destroytexture
setftexturenil
submitted-work-donequeue
ok
null
luv::metal-queue-pending-submissionsqueue
ok
objc:objective-c-object-released-pnative-command-buffer
ok
objc:objective-c-object-released-pallocator
ok
objc:objective-c-object-released-pnative-texture
whencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
whentexture
destroytexture
destroydevice
deftestmetal-submission-signals-its-frontier-when-presentation-raises
let*
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
encodernil
command-buffernil
native-command-buffernil
allocatornil
unwind-protect
progn
setfencodercommand-buffer
finishencoder
native-command-bufferluv::metal-native-objectcommand-buffer
allocatorluv::metal-command-buffer-allocatorcommand-buffer
ok
signals
luv::submit-metal-command-buffersqueue
'simple-errorvectorcommand-buffer
:after-commitlambda
error"presentation probe"
destroycommand-buffer
setfcommand-buffernil
submitted-work-donequeue
ok
null
luv::metal-queue-pending-submissionsqueue
ok
objc:objective-c-object-released-pnative-command-buffer
ok
objc:objective-c-object-released-pallocator
whencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
destroydevice
deftestmetal-completion-signal-failure-is-a-rooted-retry-obligation
let*
luv::*gpu-retirement-ledger-custodians*
make-hash-table:test#'eq
device
request-gpu-device
make-instance'metal-gpu-provider
queue
device-queuedevice
encodernil
command-buffernil
commit-symbol'luv.metal:commit-command-buffers
signal-symbol'luv.metal:signal-metal-event
original-commit
symbol-functioncommit-symbol
original-signal
symbol-functionsignal-symbol
commits0
signals0
fail-signal-pt
unwind-protect
progn
setfencodercommand-buffer
finishencoder
symbol-functioncommit-symbol
lambda
&restarguments
incfcommits
applyoriginal-commitarguments
symbol-functionsignal-symbol
lambda
&restarguments
incfsignals
whenfail-signal-p
setffail-signal-pnil
error"injected Metal completion signal failure"
applyoriginal-signalarguments
ok
ok
ok
ok
eq:submitted
luv::metal-command-buffer-statecommand-buffer
ok
ok
zerop
luv::metal-queue-completion-signal-enqueued-valuequeue
ok
The deterministic service pass retries only the published signal, never recommitting the native command buffers.
ok
ok
ok
submitted-work-donequeue
ok
null
luv::metal-queue-pending-submissionsqueue
ok
zerop
hash-table-countluv::*gpu-retirement-ledger-custodians*
setf
symbol-functioncommit-symbol
original-commitsymbol-functionsignal-symbol
original-signalwhencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
destroydevice
deftestmetal-finish-retains-ended-encoder-ownership-on-wrapper-failure
let*
device
request-gpu-device
make-instance'metal-gpu-provider
encoder
wrappernil
end-symbol'luv.metal:end-command-buffer
constructor-symbol'luv::make-metal-finished-command-buffer
original-end
symbol-functionend-symbol
original-constructor
symbol-functionconstructor-symbol
ends0
fail-construction-pt
unwind-protect
progn
setf
symbol-functionend-symbol
lambda
&restarguments
incfends
applyoriginal-endarguments
symbol-functionconstructor-symbol
lambda
&restarguments
whenfail-construction-p
setffail-construction-pnil
error"injected Metal command-buffer wrapper failure"
applyoriginal-constructorarguments
ok
ok
ok
eq:ended
luv::metal-encoder-stateencoder
ok
luv::metal-encoder-command-bufferencoder
ok
luv::metal-encoder-allocatorencoder
setfwrapper
finishencoder
ok
ok
eq:finished
luv::metal-encoder-stateencoder
ok
null
luv::metal-encoder-command-bufferencoder
ok
null
luv::metal-encoder-allocatorencoder
setf
symbol-functionend-symbol
original-endsymbol-functionconstructor-symbol
original-constructorwhenwrapper
destroywrapper
destroyencoder
destroydevice
deftestluvcraft-metal-frame-resources-follow-the-drawable-pool
call-with-sdl-main-thread
lambda
let
sessionnil
unwind-protect
progn
setfsession
start-luvcraft:provider
make-instance'metal-gpu-provider
:world:residency-radius0:visible-pnil:frames-per-secondnil:width160:height100let*
dotimes
index8
submitted-work-done
device-queue
luvcraft::luvcraft-session-devicesession
let*
frame-states
state-count
hash-table-countframe-states
frame-resource-count
ok
whensession
stop-luvcraftsession
deftestmetal-storage-buffers-carry-packed-words-to-mesh-pipelines
let
device
request-gpu-device
make-instance'metal-gpu-provider
termsnil
uniformnil
layoutnil
bind-groupnil
unwind-protect
progn
setftermsuniform
Sixty-four-bit words round-trip through the shared buffer.
write-bufferterms
make-array4:element-type'
unsigned-byte64
:initial-contents'1#x123456789abcdef0#xffffffffffffffff0
A one-word offset is legal for a 64-bit array; a half word is not.
ok
ok
signals'gpu-error
Storage buffers bind beside uniform buffers, by usage.
setflayout
createdevice
make-bind-group-layout-descriptor:entries'
:binding0:type:uniform-buffer
:binding1:type:storage-buffer
ok
setfbind-group
ok
whenbind-group
destroybind-group
whenuniform
destroyuniform
whenterms
destroyterms
destroydevice
deftestiosurface-round-trips-by-id-and-takes-a-metal-clear
The parent creates a surface and hands out its integer ID; a "child" (here, the same process) looks the ID up, wraps it as a Metal texture, and clears it. The parent's original reference sees the pixels.
let*
surface
id
metal:iosurface-idsurface
twin
device
request-gpu-device
make-instance'metal-gpu-provider
nativenil
texturenil
encodernil
command-buffernil
unwind-protect
progn
oktwin
ok
setfnative
metal:new-metal-texture-for-iosurface
luv::metal-native-objectdevice
twinmetal::+pixel-format-bgra8-unorm+:label"iosurface test"setftexture
adopt-native-texturedevicenative
make-texture-descriptor:size'
1616
:dimensions:2d:format:bgra8-unorm:usage':render-attachment:texture-binding
setfencoder
end-pass
begin-render-passencoder
make-render-pass-descriptor:color-attachments`
:view,texture:load-op:clear:store-op:store:clear-value
1.00.50.01.0
setfcommand-buffer
finishencoder
ok
ok
whencommand-buffer
destroycommand-buffer
whenencoder
destroyencoder
whentexture
destroytexture
whennative
destroydevice
whentwin
metal:release-iosurfacesurface
define-arithmetic-operator =
Test whether two compatible scalars are equal.
defun metal-resource-pixel-format
(format descriptor)defgeneric request-gpu-device
(provider &optional descriptor)defclass metal-gpu-provider
A provider for the system's preferred Metal device.
defgeneric create
(device descriptor)Asks the DEVICE for a handle to newly created instance of some object fulfilling the DESCRIPTOR.
defun write-texture
(queue destination data data-layout size)defgeneric destroy
(handle)Logically invalidate HANDLE immediately. Native teardown may be deferred until submitted work which captured HANDLE has completed.
defun new-metal-texture
(device width height pixel-format usage &key (storage-mode +storage-mode-private+)
label)defun retain-objective-c-object
(object)defgeneric adopt-native-texture
(device native-object owner descriptor)Wrap a platform texture and its retained OWNER in the HAL.
define-arithmetic-operator not
Logical negation of one test or raw truth value.
defun release-objective-c-object
(object)defun prepare-texture
(encoder texture usage)Prepare TEXTURE for semantic USAGE in ENCODER's following commands. The backend owns any layout transition, hazard barrier, or validation needed to realize the usage. Application code does not dispatch on the backend. #T5MQO0
define-arithmetic-operator *
Multiplication and scalar scaling.
defgeneric end-pass
(pass-encoder)defgeneric begin-render-pass
(encoder descriptor)defgeneric submit
(queue work)Schedule some command buffers on the QUEUE. Submission is asynchronous: returning does not mean the GPU has finished the work, only that the implementation retains everything the work depends on until it completes. Use SUBMITTED-WORK-DONE to wait.
defgeneric read-buffer
(buffer &key offset size)Wait for BUFFER's device queue and copy mapped bytes back to the host.
define-arithmetic-operator and
Logical conjunction of tests and raw truth values.
define-arithmetic-operator +
Addition over compatible quantities.
defun make-slug-glyph-cache
(device)defun make-world-text-run
(device glyph-cache camera target-format string font-pathname
&key (distance 8.0) (lift 3.0) (world-units-per-em 0.55))Shape STRING once and create a depth-tested world text run on DEVICE. The run owns dense placement/model data and its live pipeline; GLYPH-CACHE owns font-and-glyph device resources reusable across runs. See #QW7P96.
define-arithmetic-operator <
Test whether one compatible scalar is less than another.
defmacro define-objective-c-message
(name (selector result-type &key ownership class consumes-receiver)
&body arguments)defmacro define-shader-method
(generic-function name specialized-lambda-list options &body body)Define a shader-producing method with ordinary DEFMETHOD identity. Calling the method reparses its small source form so changes to source-level abstractions participate in live rebuilding. Method replacement remains the role/stage identity watched by the MOP; abstraction revisions are tracked separately by live…
defgeneric shader-specification-for
(role stage)Return the current durable shader specification for ROLE and STAGE.
defun install-metal-live-probe-fragment
(red &key invalid-p)defun draw
(pass-encoder vertex-count
&optional (instance-count 1) (first-vertex 0) (first-instance 0))defun draw-indexed
(pass-encoder index-buffer index-format index-count
&optional (instance-count 1) (first-index 0)
(base-vertex 0) (first-instance 0))Draw indexed instances from INDEX-BUFFER. INDEX-FORMAT is :UINT16 or :UINT32. The buffer is carried by the command so recorded work owns the complete indexed-draw dependency at one boundary.
defmacro with-autorelease-pool
(() &body body)defmacro with-owned-objective-c-object
((variable form) &body body)defmacro with-unchecked-objective-c-messages
(() &body body)defun set-layer-drawable-size
(layer width height)defun layer-drawable-size
(layer)defgeneric sdl-presentation-window-flags
(presentation-api)Return the immutable SDL window flags required by PRESENTATION-API.
defgeneric sdl-presentation-api-for
(provider)Return the SDL presentation policy required by GPU PROVIDER.
defclass canvas
A native destination with a lifetime and frame clock.
defun make-sdl-canvas
(&key (title "luv canvas") (width 800) (height 600)
x y (visible-p t) (fullscreen-p nil)
(high-pixel-density-p nil)
(clock (make-demand-clock))
(time (make-lazy-clock))
(presentation-api :vulkan))Construct an unrealized SDL canvas. WIDTH or HEIGHT may be NIL, which asks the display for a size when the window is finally created.
defgeneric make-canvas-context
(canvas gpu-provider &optional configuration)Create a GPU presentation relationship between CANVAS and GPU-PROVIDER. When CONFIGURATION is omitted, return the context unconfigured.
defclass canvas-event-handler
Protocol class for objects receiving canvas events.
defun dispatch-sdl-canvas-close-request
(canvas timestamp)Offer a native close to CANVAS and apply the default immediate policy. An application returning :DEFER-CANVAS-CLOSE has begun orderly teardown on another thread; its eventual CLOSE-CANVAS call ends the loop. This lets it release resources layered above the presentation context before SDL destroys that context. …
defclass metal-gpu-shader-module
A device-compiled MSL library retaining its source document.
defclass metal-gpu-render-pipeline
A linked Metal 4 render pipeline and its draw-time depth state.
defclass metal-gpu-mesh-render-pipeline
A linked Metal 4 object/mesh pipeline with its dispatch geometry.
defun set-pipeline
(pass-encoder pipeline)defun draw-mesh-workgroups
(pass-encoder x &optional (y 1) (z 1))defun compile-msl
(specification &optional (target *metal-4-target*))defun make-live-shader-pipeline
(&key role (stage :fragment) vertex-role label device layout vertex-module
vertex-buffers target-format target-blend primitive depth-stencil)Create and install a live mathematical render pipeline. VERTEX-MODULE is borrowed when VERTEX-ROLE is NIL and STAGE is not :VERTEX. Every module compiled from ROLE or VERTEX-ROLE is owned by the returned artifact and retired on replacement or explicit release.
defun refresh-live-shader-pipeline
(artifact)defun release-live-shader-pipeline
(artifact)defun set-vertex-buffer
(pass-encoder slot buffer &key (offset 0))defgeneric submitted-work-done
(queue)Block until all work submitted to QUEUE so far has completed on the GPU.
defclass table
A simple Org table without formulas.
defun new-metal-4-argument-table
(device max-buffer-count
&key (max-texture-count 0) (max-sampler-count 0) label
(attribute-strides-p nil))defclass metal-gpu-command-encoder
A general Metal 4 command encoder which owns recording memory until FINISH.
defclass metal-gpu-command-buffer
One finished, one-shot Metal 4 command buffer and its recorded dependencies.
defun submit-metal-command-buffers
(queue command-buffers &key after-commit)Commit finished Metal work and retain its dependencies to QUEUE's frontier. AFTER-COMMIT performs the drawable signal and presentation handshake before the completion event is enqueued. Presentation is the only caller of that backend-local extension; ordinary callers use SUBMIT. #T9K4RC
defvar *gpu-retirement-custodian-service-enabled-p*
Whether retaining a queue custodian starts eventual background service.
defun commit-command-buffers
(queue command-buffers)defun service-gpu-retirement-custodians-once
()Service one registry snapshot without holding the registry lock. Returns true when any backend reports progress. Errors are diagnosed once per consecutive failure and never prevent later custodians from being serviced.
defun end-command-buffer
(command-buffer)defun make-metal-finished-command-buffer
(encoder device command-buffer allocator)defun call-with-sdl-main-thread
(function)Call FUNCTION where synchronous SDL canvas work can use the native main thread. On Darwin, a batch Lisp normally evaluates its toplevel form on the process main thread. Opening a canvas from that continuation would let Cocoa replace the continuation with its durable event loop. This boundary moves FUNCTION to a…
defun start-luvcraft
(&key
(title "luv little block world — click, look, walk")
;; NIL means "as much of this display as
;; comfortably fits"; a capture asks for the
;; exact frame it intends to write out. A
;; KMSDRM console can only present at a real
;; display mode, so the environment may pin
;; the canvas to the panel's native size.
(width (let ((value (uiop:getenv "LUVCRAFT_WIDTH")))
(and value (parse-integer value))))
(height (let ((value (uiop:getenv "LUVCRAFT_HEIGHT")))
(and value (parse-integer value))))
(frames-per-second 60)
(visible-p t)
(fullscreen-p nil)
(high-pixel-density-p t)
(world (make-empty-little-block-world))
(mesher (make-instance
'exposed-face-mesher))
(camera (make-instance 'fly-camera))
player
(selected-block *stone-block*)
(inventory (make-block-inventory))
quit-function
;; A hidden capture wanting animals in frame
;; hands in a population it has already
;; placed; the ordinary game grows its own
;; around the player as it plays.
(critters
(make-instance 'critter-population))
checkpoint-writer
(provider *gpu-provider*)
(sky-clock (make-instance 'sky-clock))
(sky-profile (make-default-sky-profile))
(shadow-diagnostic-p nil)
;; The world-text banner is a proof of the
;; Slug path, not scenery: a caller that
;; wants one asks for it, and the ordinary
;; game sky stays empty.
(world-text-string nil)
(world-text-font-pathname
(cl-dejavu:font-pathname "DejaVuSans.ttf"))
(world-text-distance 8.0)
(world-text-lift 3.0)
(world-text-units-per-em 0.55)
(video-pathname nil)
(video-distance 13.0)
(video-lift 4.5)
(video-height 5.0)
(residency-radius 6)
(publication-limit 2)
(load-schedule-limit 4)
(mesh-capture-limit 1))Open a little CPU-meshed block world. Click to capture the pointer, look with the mouse, walk with WASD, and jump with Space. Once captured, left click removes the block at the centre of view and right click places the selected block. Number keys select materials, middle click picks the targeted material, Shift…
defun wait-for-luvcraft-products
(session &key minimum (timeout 10.0))Wait outside frame encoding for a useful initial set of chunk meshes. MINIMUM defaults to nine or the whole desired set when it is smaller. The visible startup path asks only for the nearest product before its first presentation; deterministic captures wait for the broader default set.
define-arithmetic-operator -
Subtraction or unary negation.
defun render-luvcraft-frame
(session timestamp &optional sample)define-arithmetic-operator /
Division of two represented quantities.
define-arithmetic-operator <=
Test whether one compatible scalar is at most another.
defun stop-luvcraft
(session)Stop SESSION exactly once and publish its result to every caller. The sole owner attempts every named release step and closes the canvas and device last. Concurrent and later callers observe the same values or RELEASE-ERROR without releasing a native handle twice.
defclass layout
How the children of a list are arranged.
define-condition gpu-error
Base condition for errors exposed by the luv GPU API.
defun create-iosurface
(width height &key (bytes-per-element 4)
(pixel-format +iosurface-pixel-format-bgra+)
(global-p t))Create a WIDTH x HEIGHT IOSurface and return its raw IOSurfaceRef. The caller owns one CF reference; release it with RELEASE-IOSURFACE. GLOBAL-P (deprecated by Apple, still honoured) is what lets another process find the surface by its integer ID with LOOKUP-IOSURFACE.
defun new-metal-texture-for-iosurface
(device surface pixel-format usage &key label)defun read-iosurface-pixel
(surface x y)defun release-iosurface
(surface)
The external-owner retain was consumed, but this original native retain remains independently owned by the test.