Lines Matching defs:device
100 RADV_FROM_HANDLE(radv_device, device, _device);
103 pipeline = vk_zalloc2(&device->vk.alloc, pAllocator, sizeof(*pipeline), 8,
106 return vk_error(device, VK_ERROR_OUT_OF_HOST_MEMORY);
108 radv_pipeline_init(device, &pipeline->base, RADV_PIPELINE_LIBRARY);
813 parse_rt_stage(struct radv_device *device, const VkPipelineShaderStageCreateInfo *sinfo)
822 nir_shader *shader = radv_shader_spirv_to_nir(device, &rt_stage, &key);
1086 visit_any_hit_shaders(struct radv_device *device,
1108 nir_shader *nir_stage = parse_rt_stage(device, stage);
1117 insert_traversal_triangle_case(struct radv_device *device,
1154 nir_iadd_imm(b, build_node_to_addr(device, b, bvh_node),
1203 visit_any_hit_shaders(device, pCreateInfo, b, &inner_vars);
1240 insert_traversal_aabb_case(struct radv_device *device,
1245 nir_ssa_def *node_addr = build_node_to_addr(device, b, bvh_node);
1308 nir_shader *nir_stage = parse_rt_stage(device, stage);
1313 any_hit_stage = parse_rt_stage(device, stage);
1385 build_traversal_shader(struct radv_device *device,
1390 nir_builder b = radv_meta_init_shader(device, MESA_SHADER_COMPUTE, "rt_traversal");
1393 b.shader->info.workgroup_size[1] = device->physical_device->rt_wave_size == 64 ? 8 : 4;
1397 unsigned lanes = device->physical_device->rt_wave_size;
1462 if (!radv_emulate_rt(device->physical_device)) {
1476 insert_traversal_aabb_case(device, pCreateInfo, &b, &vars, &trav_vars, bvh_node);
1481 nir_ssa_def *instance_node_addr = build_node_to_addr(device, &b, bvh_node);
1537 result = intersect_ray_amd_software_box(device,
1563 result = intersect_ray_amd_software_tri(device,
1567 insert_traversal_triangle_case(device, pCreateInfo, &b, result, &vars, &trav_vars, bvh_node);
1607 insert_traversal(struct radv_device *device, const VkRayTracingPipelineCreateInfoKHR *pCreateInfo,
1611 nir_shader *shader = build_traversal_shader(device, pCreateInfo, vars, var_remap);
1739 create_rt_shader(struct radv_device *device, const VkRayTracingPipelineCreateInfoKHR *pCreateInfo,
1745 nir_builder b = radv_meta_init_shader(device, MESA_SHADER_COMPUTE, "rt_combined");
1748 b.shader->info.workgroup_size[1] = device->physical_device->rt_wave_size == 64 ? 8 : 4;
1765 insert_traversal(device, pCreateInfo, &b, &vars);
1780 nir_shader *nir_stage = parse_rt_stage(device, stage);
1820 RADV_FROM_HANDLE(radv_device, device, _device);
1829 (device->instance->debug_flags & RADV_DEBUG_DUMP_SHADER_STATS) || device->keep_shader_info;
1841 radv_hash_rt_shaders(hash, &local_create_info, radv_get_hash_flags(device, keep_statistic_info));
1847 .requiredSubgroupSize = device->physical_device->rt_wave_size,
1880 shader = create_rt_shader(device, &local_create_info, stack_sizes);
1930 radv_pipeline_destroy(device, pipeline, pAllocator);
1968 radv_GetRayTracingShaderGroupHandlesKHR(VkDevice device, VkPipeline _pipeline, uint32_t firstGroup,
1988 radv_GetRayTracingShaderGroupStackSizeKHR(VkDevice device, VkPipeline _pipeline, uint32_t group,
2008 RADV_FROM_HANDLE(radv_device, device, _device);
2010 return vk_error(device, VK_ERROR_FEATURE_NOT_PRESENT);