AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
998 Commits 3 Branches 0 Tags
0dadf681db8c42ccbcd70efd3caf607f00bb08cd
Commit Graph

57 Commits

Author SHA1 Message Date
Rahul Garg d304ad4e1f Removed deprecated hipMallocHost 
Change-Id: I3141fe05a34b6a306297a30721509965f49ccb97


[ROCm/hip commit: 6790ff6b11]
 2016-09-26 05:52:21 +05:30
Rahul Garg 8f68e34442 Removed deprecated hipFreeHost 
Change-Id: I9747ea3993090e0da6a2e1f5e9ce318762bc03e1


[ROCm/hip commit: 7b87a972cb]
 2016-09-26 05:35:14 +05:30
Ben Sander c845631845 Add kind translation for hipMemcpyDeviceToDevice 
[ROCm/hip commit: 0d47e62cb0]
 2016-09-22 14:21:19 -05:00
Aditya Atluri 468565058e added ipc runtime api for nvcc backend 
Change-Id: I3297c4c9db34e7bc3267fec64a6757f9ebf91905


[ROCm/hip commit: 50b78439af]
 2016-09-22 12:55:41 -05:00
Rahul Garg e729fa1dee Added hipRuntimeGetVersion function 
Change-Id: I59ec2beacb5a94439deed0dcc8eb37d6de1cc900


[ROCm/hip commit: bfc033cc3e]
 2016-09-22 15:21:23 +05:30
Rahul Garg e3f6800dfd HIP/NVCC path for hipChooseDevice 
Change-Id: I64690d7df1f5493e067c7ff5e3b39a10fcf323bb


[ROCm/hip commit: f3f0c6ae3c]
 2016-09-16 11:15:03 +05:30
Maneesh Gupta 572e0447f6 Fixed broken HIP build on NVCC path 
Change-Id: Iae9d7ba0c789475681b382c8af18bb9bd6156a52


[ROCm/hip commit: af8d308745]
 2016-09-15 17:02:37 +05:30
Aditya Atluri dfd8c4e3f2 Added async memcpy driver api for nvcc backend 
Change-Id: If401fc949b834c883cff9de74adb0d532a0fd942


[ROCm/hip commit: 1cb90bdd6a]
 2016-09-09 10:25:57 -05:00
Ben Sander 85e7d1799b add hipStreamQuery on nvcc, fix hipStreamWaitEvent for nvcc 
[ROCm/hip commit: 1f40a73ae1]
 2016-09-02 17:26:16 -05:00
Rahul Garg af9fcb7c87 Added hipDeviceTotalMem 
Change-Id: I877fbc9e4767bbd70ecd0184f5123c9bc6cbd06f


[ROCm/hip commit: 2f8d9e20b2]
 2016-09-02 15:12:50 +05:30
Rahul Garg bb215fe616 Added hipDeviceComputeCapability, hipDeviceGetPCIBusId and hipDeviceGetName 
Change-Id: Ibe2d975df796712633900ddc7b0734ec2b8ab4ec


[ROCm/hip commit: 3f5a2f8397]
 2016-09-02 14:45:53 +05:30
Ben Sander aaca975b25 add hipStreamWaitEvent on nvcc 
[ROCm/hip commit: 32e9436374]
 2016-09-01 13:28:27 -05:00
Rahul Garg b7b599f079 CUresult to hipError mapping updates 
Change-Id: I602a70acda798a47ebbbef84b438b21c399821c3


[ROCm/hip commit: 310f0660aa]
 2016-08-30 15:55:51 +05:30
Aditya Atluri 37dec666b2 added hipInit for cuInit nvcc path 
Change-Id: I594d08d936ac5d06f16e42c63062ac5776b65a0c


[ROCm/hip commit: dfc60a8359]
 2016-08-29 15:20:09 -05:00
Aditya Atluri dd8f451428 Changed module api to work with nvcc and hipcc path 
- Added cuda and cudart linking for nvcc path in hipcc
- Added hipMemcpyHtoD and hipMemcpyDtoH for nvcc path
- Changed hipDeviceptr to hipDeviceptr_t
- Fixed hipMemcpy*to* API signatues

Change-Id: I6ef076b507f92502efda475c83dcdcdd462afc37


[ROCm/hip commit: 4b377f63d0]
 2016-08-29 15:05:12 -05:00
Aditya Atluri 8e79c17ca6 Fixed nvcc path for module apis 
Change-Id: I43c7a6bc226f4f270c37f3c4af86b3b3efd0b175


[ROCm/hip commit: 9e21549139]
 2016-08-28 22:50:44 -05:00
Aditya Atluri 34257c06e6 Added NVCC support and name changes 
- Added NVCC support for module APIs
- Changed hipFunction and hipModule data types to hipFunction_t and hipModule_t
- Created new intenal ihipModuleGetFunction as it is used twice
- Changed test to match with the new data types

Change-Id: I300a1c7fd40ed7065b1b8b9de97e3a06b96ed729


[ROCm/hip commit: 8b918b065a]
 2016-08-26 10:32:01 -05:00
Rahul Garg c0a547b3fc Resolved errors due to hipCtxXXX APIs 
Change-Id: Iffac0095c4352864eca622ea318d2291571b5153


[ROCm/hip commit: ae77d4b6d7]
 2016-08-26 15:32:49 +05:30
Rahul Garg d6bdd0eafb NVCC path support for hipCtxXXX APIs 
Change-Id: Ic7dbfbdaee9d00c0de1363c50758e5e29a96a8b2


[ROCm/hip commit: 5108140087]
 2016-08-26 14:10:36 +05:30
Rahul Garg 376cc78852 Addition of hipCtxEnablePeerAccess and hipCtxDisablePeerAccess functions 
Change-Id: I381c8cbbde17eae7d9bb5d4cb1596cebf4bda039


[ROCm/hip commit: 524eb687d3]
 2016-08-26 13:51:33 +05:30
pensun e8870d2505 add occupancy support for NV path; fix hipPeekAtLastError on HCC path 
Change-Id: I26b0e1875c19d7c636ffcc18f1738926572ded81


[ROCm/hip commit: 2d228d8e0c]
 2016-08-16 16:25:03 -05:00
Aditya Atluri a873cec96c added more nvcc event functions 
Change-Id: I79ee20ef444d4c1ab6ada3c0d56730ce754ab6b6


[ROCm/hip commit: 36b81c1be6]
 2016-06-30 21:03:19 -05:00
Ben Sander 02e76a17d2 Add NVCC implementation for hipPeeakAtLastError 
[ROCm/hip commit: b0cf03114e]
 2016-06-16 09:38:34 -05:00
Ben Sander 0268c1e4e6 NVCC improvements. 
- Complete translation tables for cudaError <-> hipError_t.
- Remove some odd errors that were not correctly translated or not used.
- Add HIPCHECK_API to test infrastructure.  Used for negative testing
  an API ; if a mismatch occurs it shows the expected return error
  code.  Can also print a warning rather than error.
- Enable hipMemoryAllocate on NV system, and review error coded.
- Add hipErrorName to nvcc.

Change-Id: I680427dcf32a5796d5913cf9e7f3b4c6f6b91599

Conflicts:
	tests/src/CMakeLists.txt

Bug fixes and improved docs for hipFree and hipHostFree.

    - Passing NULL pointer initialized runtime and return hipSuccess
      (not an error like before).
    - add negative test for this. (hipMemoryAllocate, improved)
    - Match NVCC errors for invalid pointers, add to test.
    - Update hipFree and hipHostFree docs.
    - hipGetDevicePointer always set *devicePointer=NULL, even for
      invalid flags.
    - Gate shared memory usage on specific HCC work-week.

Change-Id: I533b4fd3280a3d6cdbf05eb768976f0c7506c012


[ROCm/hip commit: 2ab19ca505]
 2016-06-16 06:13:51 +05:30
Maneesh Gupta 6fdad8a80d Add hipSetDeviceFlags implementation for NVCC 
Change-Id: Id19e965950b728cfe0a514e6cdf65a191d063c10


[ROCm/hip commit: 0452d7c1af]
 2016-05-20 12:39:02 +05:30
pensun a708c400d3 Add missing cudaMemsetAsync transformation 
[ROCm/hip commit: 234727c801]
 2016-04-14 09:02:02 -05:00
pensun fa114274ac fix query of memoryClockRate and memoryBusWidth for both NV and HCC path 
[ROCm/hip commit: 535de2ecc1]
 2016-03-25 09:24:08 -05:00
Aditya Atluri 831b55129d Revert "Revert "fix nvcc for hipHostMalloc* flags."" 
This reverts commit 4bebb99566.


[ROCm/hip commit: e5918ce729]
 2016-03-21 10:39:49 -05:00
Aditya Atluri 4bebb99566 Revert "fix nvcc for hipHostMalloc* flags." 
This reverts commit 9f071dde99.


[ROCm/hip commit: 3f5eb20cf0]
 2016-03-21 10:36:14 -05:00
Ben Sander 9f071dde99 fix nvcc for hipHostMalloc* flags. 
[ROCm/hip commit: b6962826eb]
 2016-03-21 09:33:46 -05:00
Ben Sander b319209299 hipHostRegister and hipHostMalloc refactor. 
Note hipHostMalloc (not hipHostAlloc or hipMallocHost).
 -  the hipHost* is used for all HIP APIs dealing with Host memory.
    (including hipHostMalloc, hipHostFree, hipHostRegister,
hipHostUnregister, hipHostGetFlags, hipHostGetDevicePointer).
  - hipMallocHost is consistent with "hipMalloc" for allocating device
    memory.  Enumerations hipHostMalloc* also used as optional
    flags parm to hipHostMalloc.


[ROCm/hip commit: ab910efb96]
 2016-03-22 02:30:10 -05:00
Ben Sander 9c3100894c fix nvcc compiler 
- MallocHost and FreeHost deprecation.
- Change tests to call new hipHost* equivs.
- Add missing StreamSynchronize.


[ROCm/hip commit: 9941ba0bc6]
 2016-03-19 04:20:15 -05:00
Ben Sander 4c77ecef9a Deprecate hipMallocHost and hipFreeHost. 
These will print compiler warnings if used, so we can weed them out
before removing.

Also add a default flags args for hipHostAlloc, in the C++ functioin
headers.  So you can replace hipMallocHost(&ptr, size( with hipHostAlloc(&ptr, size)


[ROCm/hip commit: cea37c3e91]
 2016-03-19 22:53:59 -05:00
Aditya Atluri c05f4abd71 Added hipHostRegister flags 
[ROCm/hip commit: d9429dd4ec]
 2016-03-07 10:52:40 -06:00
Aditya Atluri 02760925a9 Added hipHostRegister feature for CUDA backend and its tests 
[ROCm/hip commit: 4ed0b1cb1a]
 2016-03-07 03:42:50 -06:00
Maneesh Gupta 2de8a1a4a6 Fix typo in nvcc_detail/hip_runtime_api.h 
[ROCm/hip commit: 39d5a2c079]
 2016-03-07 09:40:15 +05:30
Aditya Atluri 91dbc3114d added feature for hipHostGetFlags for CUDA and HIP 
[ROCm/hip commit: 75952029d6]
 2016-03-06 12:17:30 -06:00
Aditya Atluri f1b8758919 corrected hipDeviceGetProperties to hipGetDeviceProperties - not docs 
[ROCm/hip commit: d3ba2b9782]
 2016-03-06 08:31:04 -06:00
Aditya Atluri 8e0fc269d7 Added hipHostAlloc feature for CUDA 
[ROCm/hip commit: f479531be5]
 2016-03-05 13:58:56 -06:00
Aditya Atluri 5e9d9cbabf v2 Added canHostMapMemory 
[ROCm/hip commit: a5408ed7b6]
 2016-03-05 13:15:07 -06:00
Aditya Atluri 6bfbe0483a Revert "Added canMapHostMemory feature" 
This reverts commit 8b585536ef.


[ROCm/hip commit: 2ebbdd6ec5]
 2016-03-05 13:08:57 -06:00
Aditya Atluri 8b585536ef Added canMapHostMemory feature 
[ROCm/hip commit: af4edd277f]
 2016-03-05 13:06:37 -06:00
Aditya Avinash Atluri f2dfb87abf Merge pull request #4 from AMDComputeLibraries/memtracker 
hipGetPointerAttrib behavioral changes

[ROCm/hip commit: ecadb1623c]
 2016-02-27 10:51:23 -06:00
Aditya Avinash Atluri ed96744f76 Added CUDA support for hipPointerGetAttributes 
[ROCm/hip commit: 6d66bd63de]
 2016-02-26 12:33:55 -06:00
Ben Sander 193dbe4632 Merge branch 'memtracker' into privatestaging 
Conflicts:
	include/nvcc_detail/hip_runtime_api.h


[ROCm/hip commit: 369e0d7b5b]
 2016-02-26 06:17:05 -06:00
Evgeny Mankov 82900a1888 Attribute hipDeviceAttributeIsMultiGpuBoard for obtaining Device property isMultiGpuBoard is added. 
On HIP path property obtaining done through hsa_iterate_agents and counting the devices of HSA_DEVICE_TYPE_GPU type.

P.S.
On multi-boards systems it might be problems with detection what board a GPU plugged into (not tested).


[ROCm/hip commit: 57e212606d]
 2016-02-25 23:44:39 +03:00
Evgeny Mankov c3a600c63b Guard #ifdef USE_ROCR_20 is added for ROCR_20 device properties (memoryClockRate, memoryBusWidth) 
By default isn't defined.
To add ROCR_20 support HIP have to be compiled as follows: make CXX_DEFINES+=-DUSE_ROCR_20


[ROCm/hip commit: 833c9e52ad]
 2016-02-19 13:27:03 +03:00
Evgeny Mankov 4fcd9f2542 Device property memoryBusWidth implementation. 
+ Device property memoryBusWidth is added to hipDeviceProp_t struct.
+ Device attribute hipDeviceAttributeMemoryBusWidth is added to hipDeviceAttribute_t struct.
+ Tests update.


[ROCm/hip commit: 1c19dbb807]
 2016-02-18 18:15:01 +03:00
Evgeny Mankov a0cc7134e3 Device property memoryClockRate implementation. 
+ Device property memoryClockRate is added to hipDeviceProp_t struct.
+ Device attribute hipDeviceAttributeMemoryClockRate is added to hipDeviceAttribute_t struct.
+ Tests update.
+ Rename hipDevAttrConcurrentKernels to hipDeviceAttributeConcurrentKernels.


[ROCm/hip commit: 5ea8543d2e]
 2016-02-18 17:25:28 +03:00
Evgeny Mankov 8c1a0d1924 Attribute hipDevAttrConcurrentKernels for obtaining Device property concurrentKernels is added. 
[ROCm/hip commit: 2b6fda77ca]
 2016-02-18 14:34:18 +03:00