tests/cuda/lss-test.slang


1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53

//TEST:SIMPLE(filecheck=CHECK): -target cuda
//CHECK_: __global__ void __closesthit__closestHitShaderLss
//CHECK: optixGetSpherePositionAndRadius
//CHECK: optixGetLssPositionsAndRadii
//CHECK: optixIsSphereHit
//CHECK: optixIsLSSHit

//CHECK: optixHitObjectGetSpherePositionAndRadius
//CHECK: optixHitObjectGetLssPositionsAndRadii
//CHECK: optixHitObjectIsSphereHit
//CHECK: optixHitObjectIsLSSHit

//CHECK_: __global__ void __raygen__raygenShaderLSS()
//CHECK: optixHitObjectGetSpherePositionAndRadius
//CHECK: optixHitObjectGetLssPositionsAndRadii
//CHECK: optixHitObjectIsSphereHit
//CHECK: optixHitObjectIsLSSHit

struct RayPayload
{
    float4 color;
    float2x4 lssData;
    bool isSphere;
    bool isLss;
};

[shader("closesthit")]
void closestHitShaderLss(inout RayPayload payload, in BuiltInTriangleIntersectionAttributes attr)
{
    // Test TraceRay API functions
    payload.color = GetSpherePositionAndRadius();
    payload.lssData = GetLssPositionsAndRadii();
    payload.isSphere = IsSphereHit();
    payload.isLss = IsLssHit();
    
    // Test HitObject API functions
    HitObject hitObj;
    float4 sphereData = hitObj.GetSpherePositionAndRadius();
    float2x4 lssData = hitObj.GetLssPositionsAndRadii();
    bool isSphereHit = hitObj.IsSphereHit();
    bool isLssHit = hitObj.IsLssHit();
}

[shader("raygen")]
void raygenShaderLSS(inout RayPayload payload, in BuiltInTriangleIntersectionAttributes attr)
{
    // Test HitObject API functions
    HitObject hitObj;
    float4 sphereData = hitObj.GetSpherePositionAndRadius();
    float2x4 lssData = hitObj.GetLssPositionsAndRadii();
    bool isSphereHit = hitObj.IsSphereHit();
    bool isLssHit = hitObj.IsLssHit();
}