update rq unit tests
This commit is contained in:
parent
35b23ef48f
commit
6b2ae11830
@ -1,3 +1,5 @@
|
|||||||
|
#pragma clang diagnostic ignored "-Wmissing-prototypes"
|
||||||
|
|
||||||
#include <metal_stdlib>
|
#include <metal_stdlib>
|
||||||
#include <simd/simd.h>
|
#include <simd/simd.h>
|
||||||
#if __METAL_VERSION__ >= 230
|
#if __METAL_VERSION__ >= 230
|
||||||
@ -7,6 +9,30 @@ using namespace metal::raytracing;
|
|||||||
|
|
||||||
using namespace metal;
|
using namespace metal;
|
||||||
|
|
||||||
|
intersection_params spvMakeIntersectionParams(uint flags)
|
||||||
|
{
|
||||||
|
intersection_params ip;
|
||||||
|
if ((flags & 1) != 0)
|
||||||
|
ip.force_opacity(forced_opacity::opaque);
|
||||||
|
if ((flags & 2) != 0)
|
||||||
|
ip.force_opacity(forced_opacity::non_opaque);
|
||||||
|
if ((flags & 4) != 0)
|
||||||
|
ip.accept_any_intersection(true);
|
||||||
|
if ((flags & 16) != 0)
|
||||||
|
ip.set_triangle_cull_mode(triangle_cull_mode::back);
|
||||||
|
if ((flags & 32) != 0)
|
||||||
|
ip.set_triangle_cull_mode(triangle_cull_mode::front);
|
||||||
|
if ((flags & 64) != 0)
|
||||||
|
ip.set_opacity_cull_mode(opacity_cull_mode::opaque);
|
||||||
|
if ((flags & 128) != 0)
|
||||||
|
ip.set_opacity_cull_mode(opacity_cull_mode::non_opaque);
|
||||||
|
if ((flags & 256) != 0)
|
||||||
|
ip.set_geometry_cull_mode(geometry_cull_mode::triangle);
|
||||||
|
if ((flags & 512) != 0)
|
||||||
|
ip.set_geometry_cull_mode(geometry_cull_mode::bounding_box);
|
||||||
|
return ip;
|
||||||
|
}
|
||||||
|
|
||||||
struct Params
|
struct Params
|
||||||
{
|
{
|
||||||
uint ray_flags;
|
uint ray_flags;
|
||||||
@ -22,9 +48,9 @@ struct Params
|
|||||||
kernel void main0(constant Params& _18 [[buffer(1)]], raytracing::acceleration_structure<raytracing::instancing> AS0 [[buffer(0)]], raytracing::acceleration_structure<raytracing::instancing> AS1 [[buffer(2)]])
|
kernel void main0(constant Params& _18 [[buffer(1)]], raytracing::acceleration_structure<raytracing::instancing> AS0 [[buffer(0)]], raytracing::acceleration_structure<raytracing::instancing> AS1 [[buffer(2)]])
|
||||||
{
|
{
|
||||||
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> q;
|
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> q;
|
||||||
q.reset(ray(_18.origin, _18.dir, _18.tmin, _18.tmax), AS0, intersection_params());
|
q.reset(ray(_18.origin, _18.dir, _18.tmin, _18.tmax), AS0, spvMakeIntersectionParams(_18.ray_flags));
|
||||||
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> q2[2];
|
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> q2[2];
|
||||||
q2[1].reset(ray(_18.origin, _18.dir, _18.tmin, _18.tmax), AS1, intersection_params());
|
q2[1].reset(ray(_18.origin, _18.dir, _18.tmin, _18.tmax), AS1, spvMakeIntersectionParams(_18.ray_flags));
|
||||||
bool _63 = q.next();
|
bool _63 = q.next();
|
||||||
bool res = _63;
|
bool res = _63;
|
||||||
q2[0].abort();
|
q2[0].abort();
|
||||||
|
@ -1,3 +1,5 @@
|
|||||||
|
#pragma clang diagnostic ignored "-Wmissing-prototypes"
|
||||||
|
|
||||||
#include <metal_stdlib>
|
#include <metal_stdlib>
|
||||||
#include <simd/simd.h>
|
#include <simd/simd.h>
|
||||||
#if __METAL_VERSION__ >= 230
|
#if __METAL_VERSION__ >= 230
|
||||||
@ -7,6 +9,30 @@ using namespace metal::raytracing;
|
|||||||
|
|
||||||
using namespace metal;
|
using namespace metal;
|
||||||
|
|
||||||
|
intersection_params spvMakeIntersectionParams(uint flags)
|
||||||
|
{
|
||||||
|
intersection_params ip;
|
||||||
|
if ((flags & 1) != 0)
|
||||||
|
ip.force_opacity(forced_opacity::opaque);
|
||||||
|
if ((flags & 2) != 0)
|
||||||
|
ip.force_opacity(forced_opacity::non_opaque);
|
||||||
|
if ((flags & 4) != 0)
|
||||||
|
ip.accept_any_intersection(true);
|
||||||
|
if ((flags & 16) != 0)
|
||||||
|
ip.set_triangle_cull_mode(triangle_cull_mode::back);
|
||||||
|
if ((flags & 32) != 0)
|
||||||
|
ip.set_triangle_cull_mode(triangle_cull_mode::front);
|
||||||
|
if ((flags & 64) != 0)
|
||||||
|
ip.set_opacity_cull_mode(opacity_cull_mode::opaque);
|
||||||
|
if ((flags & 128) != 0)
|
||||||
|
ip.set_opacity_cull_mode(opacity_cull_mode::non_opaque);
|
||||||
|
if ((flags & 256) != 0)
|
||||||
|
ip.set_geometry_cull_mode(geometry_cull_mode::triangle);
|
||||||
|
if ((flags & 512) != 0)
|
||||||
|
ip.set_geometry_cull_mode(geometry_cull_mode::bounding_box);
|
||||||
|
return ip;
|
||||||
|
}
|
||||||
|
|
||||||
struct main0_out
|
struct main0_out
|
||||||
{
|
{
|
||||||
float4 outColor [[color(0)]];
|
float4 outColor [[color(0)]];
|
||||||
@ -21,7 +47,7 @@ fragment main0_out main0(main0_in in [[stage_in]], raytracing::acceleration_stru
|
|||||||
{
|
{
|
||||||
main0_out out = {};
|
main0_out out = {};
|
||||||
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> rayQuery;
|
raytracing::intersection_query<raytracing::instancing, raytracing::triangle_data> rayQuery;
|
||||||
rayQuery.reset(ray(float3((in.inPos.xy * 4.0) - float2(2.0), 1.0), float3(0.0, 0.0, -1.0), 0.001000000047497451305389404296875, 2.0), topLevelAS, intersection_params());
|
rayQuery.reset(ray(float3((in.inPos.xy * 4.0) - float2(2.0), 1.0), float3(0.0, 0.0, -1.0), 0.001000000047497451305389404296875, 2.0), topLevelAS, spvMakeIntersectionParams(4u));
|
||||||
for (;;)
|
for (;;)
|
||||||
{
|
{
|
||||||
bool _88 = rayQuery.next();
|
bool _88 = rayQuery.next();
|
||||||
|
Loading…
Reference in New Issue
Block a user