Method commit

modules/cpu/ISPCDevice.cpp:207–326

#endif

void ISPCDevice::commit()
{
  Device::commit();

  // Check if SYCL context and device have been provided externally
  void *appSyclCtxNew = getParam<void *>("syclContext", nullptr);
  void *appSyclDeviceNew = getParam<void *>("syclDevice", nullptr);
  if ((appSyclCtxNew && !appSyclDeviceNew)
      || (!appSyclCtxNew && appSyclDeviceNew)) {
    handleError(OSP_INVALID_OPERATION,
        "OSPRay ISPCDevice invalid configuration: if providing a syclContext and syclDevice both must be provided");
    return;
  }

  // Release all devices if user-provided parameters has changed
  if ((appSyclCtxNew != appSyclCtx) || (appSyclDeviceNew != appSyclDevice)) {
    // Release DRT device
    drtDevice.reset();

    // Release Embree device
    if (embreeDevice) {
      rtcReleaseDevice(embreeDevice);
      embreeDevice = nullptr;
    }
#ifdef OSPRAY_ENABLE_VOLUMES
    // Release VKL device
    if (vklDevice) {
      vklReleaseDevice(vklDevice);
      vklDevice = nullptr;
    }
#endif
  }

  // Save user-provided parameters
  appSyclCtx = appSyclCtxNew;
  appSyclDevice = appSyclDeviceNew;

  // We will create run-time device once only
  if (!drtDevice) {
    // Create DRT device
    if (appSyclCtx && appSyclDevice)
      drtDevice =
          devicert::make_device_unique(appSyclDevice, appSyclCtx, debugMode);
    else
      drtDevice = devicert::make_device_unique(debugMode);
  }

  if (!embreeDevice) {
#ifdef OSPRAY_TARGET_SYCL
    embreeDevice = rtcNewSYCLDevice(
        *static_cast<sycl::context *>(drtDevice->getSyclContextPtr()),
        generateEmbreeDeviceCfg(*this).c_str());
    rtcSetDeviceSYCLDevice(embreeDevice,
        *static_cast<sycl::device *>(drtDevice->getSyclDevicePtr()));
#else
    embreeDevice = rtcNewDevice(generateEmbreeDeviceCfg(*this).c_str());
#endif
    rtcSetDeviceErrorFunction(embreeDevice, embreeErrorFunc, nullptr);