Lines Matching defs:Res
89 CUresult Res = cuModuleLoadDataEx(&Module, getStart(), 0, nullptr, nullptr);
90 if (auto Err = Plugin::check(Res, "Error in cuModuleLoadDataEx: %s"))
100 CUresult Res = cuModuleUnload(Module);
101 if (auto Err = Plugin::check(Res, "Error in cuModuleUnload: %s"))
126 CUresult Res;
130 Res = cuModuleGetFunction(&Func, CUDAImage.getModule(), getName());
131 if (auto Err = Plugin::check(Res, "Error in cuModuleGetFunction('%s'): %s",
140 Res = cuFuncGetAttribute(&MaxThreads,
142 if (auto Err = Plugin::check(Res, "Error in cuFuncGetAttribute: %s"))
180 CUresult Res = cuStreamCreate(&Stream, CU_STREAM_NON_BLOCKING);
181 if (auto Err = Plugin::check(Res, "Error in cuStreamCreate: %s"))
193 CUresult Res = cuStreamDestroy(Stream);
194 if (auto Err = Plugin::check(Res, "Error in cuStreamDestroy: %s"))
227 CUresult Res = cuEventCreate(&Event, CU_EVENT_DEFAULT);
228 if (auto Err = Plugin::check(Res, "Error in cuEventCreate: %s"))
240 CUresult Res = cuEventDestroy(Event);
241 if (auto Err = Plugin::check(Res, "Error in cuEventDestroy: %s"))
268 CUresult Res = cuDeviceGet(&Device, DeviceId);
269 if (auto Err = Plugin::check(Res, "Error in cuDeviceGet: %s"))
276 Res = cuDevicePrimaryCtxGetState(Device, &FormerPrimaryCtxFlags,
279 Plugin::check(Res, "Error in cuDevicePrimaryCtxGetState: %s"))
293 Res = cuDevicePrimaryCtxSetFlags(Device, CU_CTX_SCHED_BLOCKING_SYNC);
295 Plugin::check(Res, "Error in cuDevicePrimaryCtxSetFlags: %s"))
301 Res = cuDevicePrimaryCtxRetain(&Context, Device);
302 if (auto Err = Plugin::check(Res, "Error in cuDevicePrimaryCtxRetain: %s"))
383 CUresult Res = cuDevicePrimaryCtxRelease(Device);
385 Plugin::check(Res, "Error in cuDevicePrimaryCtxRelease: %s"))
487 CUresult Res = cuCtxSetCurrent(Context);
488 return Plugin::check(Res, "Error in cuCtxSetCurrent: %s");
554 CUresult Res;
559 Res = cuMemAlloc(&DevicePtr, Size);
563 Res = cuMemAllocHost(&MemAlloc, Size);
566 Res = cuMemAllocManaged(&DevicePtr, Size, CU_MEM_ATTACH_GLOBAL);
571 if ((Res = cuStreamCreate(&Stream, CU_STREAM_NON_BLOCKING)))
573 if ((Res = cuMemAllocAsync(&DevicePtr, Size, Stream)))
576 Res = cuStreamDestroy(Stream);
582 Plugin::check(Res, "Error in cuMemAlloc[Host|Managed]: %s")) {
599 CUresult Res;
604 Res = cuMemFree((CUdeviceptr)TgtPtr);
607 Res = cuMemFreeHost(TgtPtr);
611 if ((Res = cuStreamCreate(&Stream, CU_STREAM_NON_BLOCKING)))
615 if ((Res = cuStreamDestroy(Stream)))
620 if (auto Err = Plugin::check(Res, "Error in cuMemFree[Host]: %s")) {
630 CUresult Res;
631 Res = cuStreamSynchronize(Stream);
640 return Plugin::check(Res, "Error in cuStreamSynchronize: %s");
671 CUresult Res = cuMemGetInfo(&Free, &Total);
672 if (auto Err = Plugin::check(Res, "Error in cuMemGetInfo: %s"))
689 Plugin::check(Res, "Error in cuMemGetAllocationGranularity: %s"))
700 Res = cuMemCreate(&AHandle, Size, &Prop, 0);
701 if (auto Err = Plugin::check(Res, "Error in cuMemCreate: %s"))
705 Res = cuMemAddressReserve(&DevPtr, Size, 0, DVAddr, 0);
706 if (auto Err = Plugin::check(Res, "Error in cuMemAddressReserve: %s"))
709 Res = cuMemMap(DevPtr, Size, 0, AHandle, 0);
710 if (auto Err = Plugin::check(Res, "Error in cuMemMap: %s"))
719 Res = cuMemSetAccess(DevPtr, Size, &ADesc, 1);
720 if (auto Err = Plugin::check(Res, "Error in cuMemSetAccess: %s"))
743 CUresult Res = cuMemUnmap(DVAddr, Size);
744 if (auto Err = Plugin::check(Res, "Error in cuMemUnmap: %s"))
747 Res = cuMemRelease(AllocHandle);
748 if (auto Err = Plugin::check(Res, "Error in cuMemRelease: %s"))
751 Res = cuMemAddressFree(DVAddr, Size);
752 if (auto Err = Plugin::check(Res, "Error in cuMemAddressFree: %s"))
762 CUresult Res = cuStreamQuery(Stream);
765 if (Res == CUDA_ERROR_NOT_READY)
775 return Plugin::check(Res, "Error in cuStreamQuery: %s");
802 CUresult Res = cuMemcpyHtoDAsync((CUdeviceptr)TgtPtr, HstPtr, Size, Stream);
803 return Plugin::check(Res, "Error in cuMemcpyHtoDAsync: %s");
816 CUresult Res = cuMemcpyDtoHAsync(HstPtr, (CUdeviceptr)TgtPtr, Size, Stream);
817 return Plugin::check(Res, "Error in cuMemcpyDtoHAsync: %s");
876 CUresult Res = cuEventRecord(Event, Stream);
877 return Plugin::check(Res, "Error in cuEventRecord: %s");
892 CUresult Res = cuStreamWaitEvent(Stream, Event, 0);
893 return Plugin::check(Res, "Error in cuStreamWaitEvent: %s");
899 CUresult Res = cuEventSynchronize(Event);
900 return Plugin::check(Res, "Error in cuEventSynchronize: %s");
910 CUresult Res = cuDriverGetVersion(&TmpInt);
911 if (Res == CUDA_SUCCESS)
916 Res = cuDeviceGetName(TmpChar, 1000, Device);
917 if (Res == CUDA_SUCCESS)
920 Res = cuDeviceTotalMem(&TmpSt, Device);
921 if (Res == CUDA_SUCCESS)
924 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MULTIPROCESSOR_COUNT, TmpInt);
925 if (Res == CUDA_SUCCESS)
928 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_GPU_OVERLAP, TmpInt);
929 if (Res == CUDA_SUCCESS)
932 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_TOTAL_CONSTANT_MEMORY, TmpInt);
933 if (Res == CUDA_SUCCESS)
936 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK,
938 if (Res == CUDA_SUCCESS)
941 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_REGISTERS_PER_BLOCK, TmpInt);
942 if (Res == CUDA_SUCCESS)
945 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_WARP_SIZE, TmpInt);
946 if (Res == CUDA_SUCCESS)
949 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_BLOCK, TmpInt);
950 if (Res == CUDA_SUCCESS)
954 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_X, TmpInt);
955 if (Res == CUDA_SUCCESS)
957 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Y, TmpInt);
958 if (Res == CUDA_SUCCESS)
960 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Z, TmpInt);
961 if (Res == CUDA_SUCCESS)
965 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_X, TmpInt);
966 if (Res == CUDA_SUCCESS)
968 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Y, TmpInt);
969 if (Res == CUDA_SUCCESS)
971 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Z, TmpInt);
972 if (Res == CUDA_SUCCESS)
975 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_PITCH, TmpInt);
976 if (Res == CUDA_SUCCESS)
979 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_TEXTURE_ALIGNMENT, TmpInt);
980 if (Res == CUDA_SUCCESS)
983 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_CLOCK_RATE, TmpInt);
984 if (Res == CUDA_SUCCESS)
987 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_KERNEL_EXEC_TIMEOUT, TmpInt);
988 if (Res == CUDA_SUCCESS)
991 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_INTEGRATED, TmpInt);
992 if (Res == CUDA_SUCCESS)
995 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_CAN_MAP_HOST_MEMORY, TmpInt);
996 if (Res == CUDA_SUCCESS)
999 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_COMPUTE_MODE, TmpInt);
1000 if (Res == CUDA_SUCCESS) {
1012 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_CONCURRENT_KERNELS, TmpInt);
1013 if (Res == CUDA_SUCCESS)
1016 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_ECC_ENABLED, TmpInt);
1017 if (Res == CUDA_SUCCESS)
1020 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MEMORY_CLOCK_RATE, TmpInt);
1021 if (Res == CUDA_SUCCESS)
1024 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_GLOBAL_MEMORY_BUS_WIDTH, TmpInt);
1025 if (Res == CUDA_SUCCESS)
1028 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_L2_CACHE_SIZE, TmpInt);
1029 if (Res == CUDA_SUCCESS)
1032 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_MULTIPROCESSOR,
1034 if (Res == CUDA_SUCCESS)
1037 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_ASYNC_ENGINE_COUNT, TmpInt);
1038 if (Res == CUDA_SUCCESS)
1041 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_UNIFIED_ADDRESSING, TmpInt);
1042 if (Res == CUDA_SUCCESS)
1045 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MANAGED_MEMORY, TmpInt);
1046 if (Res == CUDA_SUCCESS)
1049 Res =
1051 if (Res == CUDA_SUCCESS)
1054 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_COMPUTE_PREEMPTION_SUPPORTED,
1056 if (Res == CUDA_SUCCESS)
1059 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_COOPERATIVE_LAUNCH, TmpInt);
1060 if (Res == CUDA_SUCCESS)
1063 Res = getDeviceAttrRaw(CU_DEVICE_ATTRIBUTE_MULTI_GPU_BOARD, TmpInt);
1064 if (Res == CUDA_SUCCESS)
1091 CUresult Res = cuDeviceTotalMem(&Value, Device);
1092 return Plugin::check(Res, "Error in getDeviceMemorySize %s");
1097 CUresult Res = cuCtxSetLimit(Kind, Value);
1098 return Plugin::check(Res, "Error in cuCtxSetLimit: %s");
1101 CUresult Res = cuCtxGetLimit(&Value, Kind);
1102 return Plugin::check(Res, "Error in cuCtxGetLimit: %s");
1108 CUresult Res =
1110 return Plugin::check(Res, "Error in cuDeviceGetAttribute: %s");
1279 CUresult Res = cuLaunchKernel(Func, NumBlocks[0], NumBlocks[1], NumBlocks[2],
1293 return Plugin::check(Res, "Error in cuLaunchKernel for '%s': %s", getName());
1311 CUresult Res =
1313 if (auto Err = Plugin::check(Res, "Error in cuModuleGetGlobal for '%s': %s",
1338 CUresult Res = cuInit(0);
1339 if (Res == CUDA_ERROR_INVALID_HANDLE) {
1345 if (Res == CUDA_ERROR_NO_DEVICE) {
1351 if (auto Err = Plugin::check(Res, "Error in cuInit: %s"))
1356 Res = cuDeviceGetCount(&NumDevices);
1357 if (auto Err = Plugin::check(Res, "Error in cuDeviceGetCount: %s"))
1404 CUresult Res = cuDeviceGet(&Device, DeviceId);
1405 if (auto Err = Plugin::check(Res, "Error in cuDeviceGet: %s"))
1409 Res = cuDeviceGetAttribute(
1411 if (auto Err = Plugin::check(Res, "Error in cuDeviceGetAttribute: %s"))
1414 Res = cuDeviceGetAttribute(
1416 if (auto Err = Plugin::check(Res, "Error in cuDeviceGetAttribute: %s"))
1438 CUresult Res;
1457 Res = cuDeviceCanAccessPeer(&CanAccessPeer, Device, DstDevice.Device);
1458 if (auto Err = Plugin::check(Res, "Error in cuDeviceCanAccessPeer: %s"))
1462 Res = cuCtxEnablePeerAccess(DstDevice.Context, 0);
1463 if (Res == CUDA_ERROR_TOO_MANY_PEERS) {
1468 Plugin::check(Res, "Error in cuCtxEnablePeerAccess: %s"))
1483 Res = cuMemcpyPeerAsync(CUDstPtr, Context, CUSrcPtr, DstDevice.Context,
1485 return Plugin::check(Res, "Error in cuMemcpyPeerAsync: %s");
1489 Res = cuMemcpyDtoDAsync(CUDstPtr, CUSrcPtr, Size, Stream);
1490 return Plugin::check(Res, "Error in cuMemcpyDtoDAsync: %s");