Function removeDeviceContext

src/backend/oneapi/platform.cpp:467–520

}

void removeDeviceContext(sycl::device& dev, sycl::context& ctx) {
    if (getDevice() == dev && getContext() == ctx) {
        AF_ERROR("Cannot pop the device currently in use", AF_ERR_ARG);
    }

    DeviceManager& devMngr = DeviceManager::getInstance();

    int deleteIdx = -1;
    {
        common::lock_guard_t lock(devMngr.deviceMutex);

        const int dCount = static_cast<int>(devMngr.mDevices.size());
        for (int i = 0; i < dCount; ++i) {
            if (*devMngr.mDevices[i] == dev && *devMngr.mContexts[i] == ctx) {
                deleteIdx = i;
                break;
            }
        }
    }

    if (deleteIdx < static_cast<int>(devMngr.mUserDeviceOffset)) {
        AF_ERROR("Cannot pop ArrayFire internal devices", AF_ERR_ARG);
    } else if (deleteIdx == -1) {
        AF_ERROR("No matching device found", AF_ERR_ARG);
    } else {
        // remove memory management for device added by user outside of the lock
        memoryManager().removeMemoryManagement(deleteIdx);

        common::lock_guard_t lock(devMngr.deviceMutex);
        // FIXME: this case can potentially cause issues due to the
        // modification of the device pool stl containers.

        // IF the current active device is enumerated at a position
        // that lies ahead of the device that has been requested
        // to be removed. We just pop the entries from pool since it
        // has no side effects.
        devMngr.mDevices.erase(devMngr.mDevices.begin() + deleteIdx);
        devMngr.mContexts.erase(devMngr.mContexts.begin() + deleteIdx);
        devMngr.mQueues.erase(devMngr.mQueues.begin() + deleteIdx);
        devMngr.mPlatforms.erase(devMngr.mPlatforms.begin() + deleteIdx);

        // FIXME: add OpenGL Interop for user provided contexts later
        devMngr.mIsGLSharingOn.erase(devMngr.mIsGLSharingOn.begin() +
                                     deleteIdx);

        // OTHERWISE, update(decrement) the thread local active device ids
        device_id_t& devId = tlocalActiveDeviceId();

        if (deleteIdx < static_cast<int>(devId.first)) {
            device_id_t newVals = make_pair(devId.first - 1, devId.second - 1);
            devId               = newVals;
        }
    }
}

unsigned getMemoryBusWidth(const sycl::device& device) {
    return device.get_info<sycl::info::device::global_mem_cache_line_size>();