@@ -236,7 +236,8 @@ QMgrHelper::getQueue (DPCTLSyclBackendType BETy,
236
236
QRef = new queue (gpuQs[DNum]);
237
237
break ;
238
238
}
239
- case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO | DPCTLSyclDeviceType::DPCTL_GPU:
239
+ case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO |
240
+ DPCTLSyclDeviceType::DPCTL_GPU:
240
241
{
241
242
auto l0GpuQs = get_level0_gpu_queues ();
242
243
if (DNum >= l0GpuQs.size ()) {
@@ -316,7 +317,8 @@ QMgrHelper::setAsDefaultQueue (DPCTLSyclBackendType BETy,
316
317
activeQ[0 ] = oclgpu_q[DNum];
317
318
break ;
318
319
}
319
- case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO | DPCTLSyclDeviceType::DPCTL_GPU:
320
+ case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO |
321
+ DPCTLSyclDeviceType::DPCTL_GPU:
320
322
{
321
323
auto l0gpu_q = get_level0_gpu_queues ();
322
324
if (DNum >= l0gpu_q.size ()) {
@@ -342,8 +344,8 @@ QMgrHelper::setAsDefaultQueue (DPCTLSyclBackendType BETy,
342
344
/* !
343
345
* Allocates a new sycl::queue by copying from the cached {cpu|gpu}_queues
344
346
* vector. The pointer returned is now owned by the caller and must be properly
345
- * cleaned up. The helper function DPCTLDeleteSyclQueue() can be used is for that
346
- * purpose.
347
+ * cleaned up. The helper function DPCTLDeleteSyclQueue() can be used is for
348
+ * that purpose.
347
349
*/
348
350
__dpctl_give DPCTLSyclQueueRef
349
351
QMgrHelper::pushSyclQueue (DPCTLSyclBackendType BETy,
@@ -383,7 +385,8 @@ QMgrHelper::pushSyclQueue (DPCTLSyclBackendType BETy,
383
385
QRef = new queue (activeQ[get_active_queues ().size ()-1 ]);
384
386
break ;
385
387
}
386
- case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO | DPCTLSyclDeviceType::DPCTL_GPU:
388
+ case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO |
389
+ DPCTLSyclDeviceType::DPCTL_GPU:
387
390
{
388
391
if (DNum >= get_level0_gpu_queues ().size ()) {
389
392
// \todo handle error
@@ -447,7 +450,7 @@ size_t DPCTLQueueMgr_GetNumActivatedQueues ()
447
450
* type combination.
448
451
*/
449
452
size_t DPCTLQueueMgr_GetNumQueues (DPCTLSyclBackendType BETy,
450
- DPCTLSyclDeviceType DeviceTy)
453
+ DPCTLSyclDeviceType DeviceTy)
451
454
{
452
455
switch (BETy|DeviceTy)
453
456
{
@@ -459,7 +462,8 @@ size_t DPCTLQueueMgr_GetNumQueues (DPCTLSyclBackendType BETy,
459
462
{
460
463
return QMgrHelper::get_opencl_gpu_queues ().size ();
461
464
}
462
- case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO | DPCTLSyclDeviceType::DPCTL_GPU:
465
+ case DPCTLSyclBackendType::DPCTL_LEVEL_ZERO |
466
+ DPCTLSyclDeviceType::DPCTL_GPU:
463
467
{
464
468
return QMgrHelper::get_level0_gpu_queues ().size ();
465
469
}
@@ -485,8 +489,8 @@ DPCTLSyclQueueRef DPCTLQueueMgr_GetCurrentQueue ()
485
489
* and device number. A runtime_error gets thrown if no such device exists.
486
490
*/
487
491
DPCTLSyclQueueRef DPCTLQueueMgr_GetQueue (DPCTLSyclBackendType BETy,
488
- DPCTLSyclDeviceType DeviceTy,
489
- size_t DNum)
492
+ DPCTLSyclDeviceType DeviceTy,
493
+ size_t DNum)
490
494
{
491
495
return QMgrHelper::getQueue (BETy, DeviceTy, DNum);
492
496
}
@@ -506,8 +510,8 @@ bool DPCTLQueueMgr_IsCurrentQueue (__dpctl_keep const DPCTLSyclQueueRef QRef)
506
510
*/
507
511
__dpctl_give DPCTLSyclQueueRef
508
512
DPCTLQueueMgr_SetAsDefaultQueue (DPCTLSyclBackendType BETy,
509
- DPCTLSyclDeviceType DeviceTy,
510
- size_t DNum)
513
+ DPCTLSyclDeviceType DeviceTy,
514
+ size_t DNum)
511
515
{
512
516
return QMgrHelper::setAsDefaultQueue (BETy, DeviceTy, DNum);
513
517
}
@@ -517,8 +521,8 @@ DPCTLQueueMgr_SetAsDefaultQueue (DPCTLSyclBackendType BETy,
517
521
*/
518
522
__dpctl_give DPCTLSyclQueueRef
519
523
DPCTLQueueMgr_PushQueue (DPCTLSyclBackendType BETy,
520
- DPCTLSyclDeviceType DeviceTy,
521
- size_t DNum)
524
+ DPCTLSyclDeviceType DeviceTy,
525
+ size_t DNum)
522
526
{
523
527
return QMgrHelper::pushSyclQueue (BETy, DeviceTy, DNum);
524
528
}
@@ -536,8 +540,10 @@ void DPCTLQueueMgr_PopQueue ()
536
540
* SYCL device.
537
541
*/
538
542
DPCTLSyclQueueRef
539
- DPCTLQueueMgr_GetQueueFromContextAndDevice (__dpctl_keep DPCTLSyclContextRef CRef,
540
- __dpctl_keep DPCTLSyclDeviceRef DRef)
543
+ DPCTLQueueMgr_GetQueueFromContextAndDevice (
544
+ __dpctl_keep DPCTLSyclContextRef CRef,
545
+ __dpctl_keep DPCTLSyclDeviceRef DRef
546
+ )
541
547
{
542
548
auto dev = unwrap (DRef);
543
549
auto ctx = unwrap (CRef);
0 commit comments