Allow render-test to run inline ray tracing tests. (shader-slang#1903)

* Update VS projects to 2019.

* Empty commit to trigger build

* Implement gfx inline ray tracing on D3D12.

* Allow render-test to run inline ray tracing tests.

Co-authored-by: Yong He <yhe@nvidia.com>

Author: csyonghe

tests/compute/ray-tracing-inline.slang

@@ -0,0 +1,47 @@
+//TEST(compute):COMPARE_COMPUTE:-d3d12 -output-using-type -use-dxil -profile sm_6_5 -render-feature ray-tracing
+//TEST(compute):COMPARE_COMPUTE:-vk -output-using-type -render-feature ray-tracing
+
+//TEST_INPUT: set scene = AccelerationStructure
+uniform RaytracingAccelerationStructure scene;
+
+//TEST_INPUT:set outputBuffer = out ubuffer(data=[0], stride=4)
+RWStructuredBuffer<float> outputBuffer;
+
+bool traceRayClosestHit(
+    float3 rayOrigin,
+    float3 rayDir,
+    out float t)
+{
+    RayDesc ray;
+    ray.Origin = rayOrigin;
+    ray.TMin = 0.01f;
+    ray.Direction = rayDir;
+    ray.TMax = 1e4f;
+    RayQuery<RAY_FLAG_NONE> q;
+    let rayFlags = RAY_FLAG_NONE;
+
+    q.TraceRayInline(
+        scene,
+        rayFlags,
+        0xff,
+        ray);
+
+    q.Proceed();
+    if(q.CommittedStatus() == COMMITTED_TRIANGLE_HIT)
+    {
+        t = q.CommittedRayT();
+        //primitiveIndex = q.CommittedPrimitiveIndex();
+        return true;
+    }
+    return false;
+}
+
+[shader("compute")]
+[numthreads(1,1,1)]
+void computeMain(
+    uint3 threadIdx : SV_DispatchThreadID)
+{
+    float t = 0.0;
+    traceRayClosestHit(float3(0.1, 0.1, 0.0), float3(0,0,1), t);
+    outputBuffer[threadIdx.x] = t;
+}

tests/compute/ray-tracing-inline.slang.expected.txt

@@ -0,0 +1,2 @@
+type: float
+0.5

tools/gfx/d3d12/render-d3d12.cpp

@@ -4316,6 +4316,22 @@ Result D3D12Device::initialize(const Desc& desc)
                 auto minPrecisionSupport = options.MinPrecisionSupport;
             }
         }
+        // Check ray tracing support
+        {
+            D3D12_FEATURE_DATA_D3D12_OPTIONS5 options;
+            if (SLANG_SUCCEEDED(m_device->CheckFeatureSupport(
+                    D3D12_FEATURE_D3D12_OPTIONS5, &options, sizeof(options))))
+            {
+                if (options.RaytracingTier != D3D12_RAYTRACING_TIER_NOT_SUPPORTED)
+                {
+                    m_features.add("ray-tracing");
+                }
+                if (options.RaytracingTier >= D3D12_RAYTRACING_TIER_1_1)
+                {
+                    m_features.add("ray-query");
+                }
+            }
+        }
     }
 
     m_desc = desc;

tools/gfx/debug-layer.cpp

@@ -228,7 +228,7 @@ void validateAccelerationStructureBuildInputs(
                     default:
                         GFX_DIAGNOSE_ERROR(
                             "Unsupported IAccelerationStructure::TriangleDesc::indexFormat. Valid "
-                            "values are R_UInt32 or R_UInt16.");
+                            "values are Unknown, R_UInt32 or R_UInt16.");
                     }
                     if (!buildInputs.geometryDescs[i].content.triangles.indexData)
                     {
@@ -237,6 +237,39 @@ void validateAccelerationStructureBuildInputs(
                             "IAccelerationStructure::TriangleDesc::indexCount is not 0");
                     }
                 }
+                if (buildInputs.geometryDescs[i].content.triangles.indexFormat != Format::Unknown)
+                {
+                    if (buildInputs.geometryDescs[i].content.triangles.indexCount == 0)
+                    {
+                        GFX_DIAGNOSE_ERROR(
+                            "IAccelerationStructure::TriangleDesc::indexCount cannot be 0 if "
+                            "IAccelerationStructure::TriangleDesc::indexFormat is not Format::Unknown");
+                    }
+                    if (buildInputs.geometryDescs[i].content.triangles.indexData == 0)
+                    {
+                        GFX_DIAGNOSE_ERROR(
+                            "IAccelerationStructure::TriangleDesc::indexData cannot be null if "
+                            "IAccelerationStructure::TriangleDesc::indexFormat is not "
+                            "Format::Unknown");
+                    }
+                }
+                else
+                {
+                    if (buildInputs.geometryDescs[i].content.triangles.indexCount != 0)
+                    {
+                        GFX_DIAGNOSE_ERROR(
+                            "IAccelerationStructure::TriangleDesc::indexCount must be 0 if "
+                            "IAccelerationStructure::TriangleDesc::indexFormat is "
+                            "Format::Unknown");
+                    }
+                    if (buildInputs.geometryDescs[i].content.triangles.indexData != 0)
+                    {
+                        GFX_DIAGNOSE_ERROR(
+                            "IAccelerationStructure::TriangleDesc::indexData must be null if "
+                            "IAccelerationStructure::TriangleDesc::indexFormat is "
+                            "Format::Unknown");
+                    }
+                }
                 if (!buildInputs.geometryDescs[i].content.triangles.vertexData)
                 {
                     GFX_DIAGNOSE_ERROR(

tools/gfx/vulkan/render-vk.cpp

@@ -5552,6 +5552,7 @@ Result VKDevice::initVulkanInstanceAndDevice(bool useValidationLayer)
             deviceCreateInfo.pNext = &rayQueryFeatures;
             deviceExtensions.add(VK_KHR_RAY_QUERY_EXTENSION_NAME);
             m_features.add("ray-query");
+            m_features.add("ray-tracing");
         }
 
         if (bufferDeviceAddressFeatures.bufferDeviceAddress)

tools/gfx/vulkan/vk-util.cpp

@@ -262,6 +262,9 @@ Result AccelerationStructureBuildGeometryInfoBuilder::build(
                 case Format::R_UInt16:
                     vkGeomData.triangles.indexType = VK_INDEX_TYPE_UINT16;
                     break;
+                case Format::Unknown:
+                    vkGeomData.triangles.indexType = VK_INDEX_TYPE_NONE_KHR;
+                    break;
                 default:
                     debugCallback->handleMessage(
                         DebugMessageType::Error,