| 254 | }; |
| 255 | |
| 256 | devicert::AsyncEvent LiveDenoiseFrameOpSharedSycl::process() |
| 257 | { |
| 258 | updateFilters(); |
| 259 | |
| 260 | // Using SYCL calls without SYCL, that's supported in C99 API only |
| 261 | |
| 262 | if (prefilter) { |
| 263 | if (filterNormal) |
| 264 | oidnExecuteSYCLFilterAsync(filterNormal.getHandle(), nullptr, 0, nullptr); |
| 265 | if (filterAlbedo) |
| 266 | oidnExecuteSYCLFilterAsync(filterAlbedo.getHandle(), nullptr, 0, nullptr); |
| 267 | } |
| 268 | |
| 269 | if (denoiser->denoiseAlpha) |
| 270 | oidnExecuteSYCLFilterAsync(filterAlpha.getHandle(), nullptr, 0, nullptr); |
| 271 | else |
| 272 | bufferOut.writeAsync(0, |
| 273 | fbView.viewDims.long_product() * sizeof(vec4f), |
| 274 | fbView.colorBufferInput); |
| 275 | |
| 276 | devicert::AsyncEvent event = denoiser->drtDevice.createAsyncEvent(); |
| 277 | |
| 278 | oidnExecuteSYCLFilterAsync( |
| 279 | filter.getHandle(), nullptr, 0, (sycl::event *)event.getSyclEventPtr()); |
| 280 | |
| 281 | return event; |
| 282 | } |
| 283 | |
| 284 | struct OSPRAY_MODULE_DENOISER_EXPORT LiveDenoiseFrameOpSharedCpu |
| 285 | : public LiveDenoiseFrameOpShared |
nothing calls this directly
no test coverage detected