| 720 | } |
| 721 | |
| 722 | sycl::event AccelBuffer::commit(sycl::queue queue) |
| 723 | { |
| 724 | if (unifiedMemory) { |
| 725 | hwaccel = (char*)accelBufferShared.data(); |
| 726 | return sycl::event(); |
| 727 | } |
| 728 | |
| 729 | auto deviceGPU = reinterpret_cast<DeviceGPU*>(device); |
| 730 | if (!deviceGPU) { |
| 731 | return sycl::event(); |
| 732 | } |
| 733 | |
| 734 | if (accelBufferDevice.size() != accelBufferHost.size()) |
| 735 | accelBufferDevice.resize(accelBufferHost.size()); |
| 736 | |
| 737 | sycl::event event = queue.memcpy(accelBufferDevice.data(), accelBufferHost.data(), accelBufferHost.size()); |
| 738 | |
| 739 | hwaccel = (char*)accelBufferDevice.data(); |
| 740 | |
| 741 | return event; |
| 742 | } |
| 743 | |
| 744 | } |
no test coverage detected