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

1589 Commits

Author SHA1 Message Date
Aditya Atluri feca2ed0dc added gfx900 to hipDeviceProp_t 
Change-Id: I49e7a32f218926fd55f1c94c5dc2366d6c8ac4ca


[ROCm/clr commit: a6dc00f167]
 2017-05-12 21:43:34 -05:00
Ben Sander 0d3c99eb6e Remove old USE_ switches no longer needed. 
[ROCm/clr commit: c7c62dd022]
 2017-05-12 16:06:03 -05:00
Ben Sander 9b222c0ae4 Add hipEventDisableSystemRelease flag. 
[ROCm/clr commit: 2c2625cb9e]
 2017-05-12 16:06:03 -05:00
Evgeny Mankov 42292df1a3 [HIPIFY] Fix string routines. 
Some Clang tooling functions return std::string, some return StringRef. Assigning of returning std::string to StringRef variables leads to garbage in it.
DEBUG build is always affected.


[ROCm/clr commit: aa52b94be1]
 2017-05-11 21:50:36 +03:00
Ben Sander 90e5930923 hipHostMalloc allocation are mapped to all devices by default. 
Support hipHostMallocPortable flag.
Default flags are hipHostMallocPortable | hipHostMallocMapped.

Also:
-refactor tests to move addCount and addCountReverse into HipTest
namespace.
-test multi-GPU host memory.


[ROCm/clr commit: ff9bed6535]
 2017-05-10 17:34:36 -05:00
Ben Sander 501d0b3161 Fix hipStreamWaitEvent for single GPU. 
[ROCm/clr commit: ae9fdf9bc1]
 2017-05-10 13:23:49 -05:00
Aditya Atluri b5f0a9471d added guard against hip_runtime.h so that non-hcc compilers can use it 
Change-Id: I3d68deda9ce8a5956e21e15a69e549d6c21e3e39


[ROCm/clr commit: 14930dc594]
 2017-05-09 10:14:16 -05:00
Ben Sander fa1ac559cb Fix some typos, add additional guidance for -BSymbolic 
[ROCm/clr commit: 9a026b62a8]
 2017-05-05 17:29:04 -05:00
Ben Sander 4afda1720d Refactor hipHostRegister test. 
Run all tests in one command.
Run 128 offsets.


[ROCm/clr commit: e417eb5d35]
 2017-05-05 17:29:04 -05:00
Ben Sander 48fdf2fc93 Update streamEventTEst. 
- add checks for events across devices.
- refactor test to make sure it runs long enough to sensitive sync
  techniques.
- add tests for DeviceSync, streamWaitEvent.


[ROCm/clr commit: 444e4a20ba]
 2017-05-05 17:29:04 -05:00
wsttiger 618f4bf702 Improve hipStreamWaitEvent test. 
- use addOne kernel, use local initializer rather than init_array.
- use addOneReverse test to add from back of array.  Test alternate fwd and backward to stress dependency logic.
- check device-side dependencies.


[ROCm/clr commit: a10d37e5e6]
 2017-05-05 17:29:04 -05:00
Evgeny Mankov 3028345953 [HIPIFY] LLVM 3.9 support 
3.8 and 3.9 are both supported. 3.8 is stable, 3.9 needs more testing.


[ROCm/clr commit: 054bf0859d]
 2017-05-05 21:28:02 +03:00
Rahul Garg ba1a3360ab hipMemcpy2DAsync for HIP/NVCC 
Change-Id: I46f0057fef49bdaaac41c1df80c3e27432b8f376


[ROCm/clr commit: f77059218c]
 2017-05-04 06:47:55 +05:30
Evgeny Mankov e9ad0f3b00 [HIPIFY] CUDA RT memcpy functions update. 
cudaMemcpyFromSymbol -> hipMemcpyFromSymbol
cudaMemcpyFromSymbolAsync -> hipMemcpyFromSymbolAsync
cudaMemcpy2DAsync -> hipMemcpy2DAsync


[ROCm/clr commit: 2636d91ba4]
 2017-05-03 23:05:44 +03:00
Evgeny Mankov df05e96760 [HIPIFY] Blas update: add a few functions, supported by HIP. 
cublasDaxpy -> hipblasDaxpy
cublasDgemv -> hipblasDgemv
cublasDger  -> hipblasDger
cublasDgemm -> hipblasDgemm
cublasDgemmBatched -> hipblasDgemmBatched
cublasGetStream -> hipblasGetStream
cublasSetStream -> hipblasSetStream
cublasDaxpy -> hipblasDaxpy


[ROCm/clr commit: 72df25a0c7]
 2017-05-03 22:45:56 +03:00
Evgeny Mankov 3ca552c669 [HIPIFY] HIPIFY and HIP sync with CUDA Driver API data types. 
+ Update CUDA_Driver_API_functions_supported_by_HIP.md.
+ Final update of HIPIFY with CUDA driver data types.

[TODO] Syncing HIPIFY and HIP by CUDA Driver API functions.


[ROCm/clr commit: 3b40776244]
 2017-05-03 21:59:48 +03:00
Rahul Garg 9739d5d60f Added support for hipMemcpy2DAsync in HIP/HCC 
Change-Id: Ia4a8306f2dc1e33a81a7195ec29aef652fcccc4b


[ROCm/clr commit: b136e80a45]
 2017-05-03 22:29:12 +05:30
Evgeny Mankov 03595a9883 [HIPIFY] Rename enumConstantDecl -> enumDecl 
Reason: not to mix up with clang's enumConstantDecl, used for enum DeclRefExpr (enum constant).


[ROCm/clr commit: 3e89277a9b]
 2017-04-28 21:59:33 +03:00
Evgeny Mankov 3252416883 * [HIPIFY] [FIX] Replacement error: enum cudaMemcpyKind kind -> hipMemcpyKindyKind kind 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/72

[Solution] [Workaround]
Offset calculation for enum VarDecl as param decl, declared with enum type specifier.

[Result]
enum cudaMemcpyKind kind -> enum hipMemcpyKind kind

[ToDo]
Test on terminal qualifiers (const, etc).


[ROCm/clr commit: 85a32c3987]
 2017-04-28 21:45:36 +03:00
Evgeny Mankov 3e06497eaa [HIPIFY] [FIX] replacement error: cudaError_t -> hipError_t_t 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/71

[Solution]
getUnqualifiedType for enumConstantDecl's type is added, except ordinary enum declarations (w/o typedef).

[ToDo]
Find more appropriate way of distinguishing redefined enum declarations and ordinary ones.


[ROCm/clr commit: 5f76cf3098]
 2017-04-28 21:03:03 +03:00
Aditya Atluri 6dccc18fa0 fixed hipFuncSetCacheConfig on rocm path 
Change-Id: I937a3afbf115edc94a753a0beb2230ed60a6f021


[ROCm/clr commit: 208bdbbcbb]
 2017-04-28 11:53:11 -05:00
Aditya Atluri c662b426dc fixed fast math expf and exp10f 
Change-Id: I73963220f902efebb0a7404c5f8966dffb4c35ca


[ROCm/clr commit: f368271872]
 2017-04-26 19:01:10 -05:00
Aditya Atluri afec5e075b added hipFuncSetCacheConfig API for nvcc path 
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d


[ROCm/clr commit: e91c35fde0]
 2017-04-26 18:56:57 -05:00
Maneesh Gupta f5f4850297 Merge branch 'amd-master' into amd-develop 
[ROCm/clr commit: a5fb13bab3]
 2017-04-26 23:55:13 +05:30
Sun, Peng a82ecbcc13 fix hip_complex.h header on NV path 
Change-Id: Ia95d003ca1b284bab1c76723050e6b3b89178f65


[ROCm/clr commit: 50daa408aa]
 2017-04-25 00:15:20 -05:00
Ben Sander 579b8e5050 Add host offset checking 
[ROCm/clr commit: fbf28a8728]
 2017-04-24 22:30:54 -05:00
Ben Sander 20315571bd Refactor hipHostRegister test. 
- Add more testing for offsets.
- Parse cmdline options and use --tests.


[ROCm/clr commit: e7af4ef641]
 2017-04-24 22:30:54 -05:00
Ben Sander aa4c89380e Refactor hipHostRegister to cover misaligned cases. 
[ROCm/clr commit: 5ba167b82b]
 2017-04-24 22:30:54 -05:00
Ben Sander 0e042a1529 Tailor pointer info for src/dst before calling HCC copy routines. 
HCC sometimes uses the srcPtrInfo or dstPtrInfo to determine the
pointer.  Make sure these use the actual pointer and not the base
of the allocation.


[ROCm/clr commit: 3da8e94cbf]
 2017-04-24 22:30:54 -05:00
Ben Sander 67383ddb5c Add test for non-page-aligned mem copies. 
[ROCm/clr commit: d120b2dd12]
 2017-04-24 22:30:54 -05:00
Ben Sander 37fcb3bd13 Add corrected test for offsets 
[ROCm/clr commit: b44a3eefd1]
 2017-04-24 22:30:54 -05:00
Ben Sander 04082c14a7 Refactor hipMemcpy test to share mem alloc for multiple copies. 
[ROCm/clr commit: 6b16f56f38]
 2017-04-24 22:30:54 -05:00
Ben Sander 88fa748893 Add negative testing for memory full condition. 
[ROCm/clr commit: 693e5abc1c]
 2017-04-24 22:30:54 -05:00
Ben Sander eef8282c96 Fix hip debug for case where copyAgent is null (host-to-host) 
[ROCm/clr commit: dfacfbb641]
 2017-04-24 22:30:54 -05:00
Ben Sander 05c136e7b8 Fix hipMalloc to return error code if allocation fails. 
[ROCm/clr commit: fb7eee01ff]
 2017-04-24 22:30:54 -05:00
Aditya Atluri 8d9e22c975 fixed build issues with hipPointerGetAttributes 
Change-Id: I3f5fbc05bdaef720884ba949075928752a070377


[ROCm/clr commit: 1f532b06f6]
 2017-04-24 15:31:07 -05:00
Aditya Atluri 119f5a1e67 changed arguments for hipPointerGetAttributes 
Change-Id: Ia7a7c4722c1f7d0a23f0e5cc3dd6dea6c01c1fd8


[ROCm/clr commit: 85c189c846]
 2017-04-24 15:24:16 -05:00
Maneesh Gupta ab6e1faf7b Merge branch 'amd-develop' into amd-master 
Change-Id: I312fb9d1181733ef5160d1e993e2ae57ced0f6b3


[ROCm/clr commit: 1186af91d7]
 2017-04-24 08:51:03 +05:30
Maneesh Gupta 2650e1fde7 Updated release notes 
Change-Id: Ia98aff420ea9d488924dce8fe9168cec9da301ab


[ROCm/clr commit: c16e0fb088]
 2017-04-24 08:48:35 +05:30
James Edwards dc0c44713f Specify full path of hip libraries in link file. 
Change-Id: I49b788f3489e7abff6b11006ff97fdfca4e5942c


[ROCm/clr commit: 197a29f142]
 2017-04-22 15:54:14 -05:00
James Edwards f1b0693479 Properly link hip cmake file into top level lib directory. 
Change-Id: I2113a86ca6985f34fd0cfb091abdbce0f632cfc2


[ROCm/clr commit: c33c84a596]
 2017-04-21 22:34:26 -05:00
Evgeny Mankov 268c7b035a [HIPIFY] [DOC] Readme.md update: Ubuntu 16.04 support 
[ROCm/clr commit: f66780f39b]
 2017-04-22 01:01:31 +03:00
Evgeny Mankov 8805f2ce66 [HIPIFY] Initial sync HIPIFY with HIP by CUDA Driver API data types. 
+ Introduce CUDA_Driver_API_functions_supported_by_HIP.md.
+ Initial update of HIPIFY with CUDA driver data types.
+ Initial sync HIP types against CUDA Driver and Runtime API types.
+ Typo fixes.


[ROCm/clr commit: 342c63d398]
 2017-04-21 21:46:30 +03:00
Ben Sander acacf26ed8 Fix compilation error with nvcc (c++ nullptr) 
[ROCm/clr commit: f1f907cb51]
 2017-04-21 09:01:34 -05:00
Sun, Peng 4ac3084503 add support of hipLaunchKernelGGL on NV path 
Change-Id: I0aeafd80c2181873be385d985f1d8ed86a98d136


[ROCm/clr commit: c224209200]
 2017-04-19 11:00:25 -05:00
Sun, Peng 6a3bee59f1 fix broken header in NV path 
Change-Id: Ia3aff2a89d9ba49547f51ce03a3304dfab58ba25


[ROCm/clr commit: ee299695a8]
 2017-04-19 10:47:40 -05:00
James Edwards 9f882824a9 Fix RPM HIP packages from specifying /opt 
Change-Id: Iec3c3b81eef4c8888d425eefc80b12488a8d20a1


[ROCm/clr commit: edfefc9aee]
 2017-04-19 12:35:42 +05:30
James Edwards 0339fbee52 Fix RPM HIP packages from specifying /opt 
Change-Id: Iec3c3b81eef4c8888d425eefc80b12488a8d20a1


[ROCm/clr commit: c5e1235f64]
 2017-04-17 23:58:34 -05:00
Maneesh Gupta 710efeea0c FindHIP: Apply remove_item on non-empty lists only 
Change-Id: Ib7fcb992d7e1bb679d4d86676fe3d980ba204815


[ROCm/clr commit: 137c04c536]
 2017-04-18 10:21:20 +05:30
Ben Sander 41b7984cd0 Update bugs - Add CreateKernel, new signature for static kerns. 
[ROCm/clr commit: 710c83b73b]
 2017-04-16 14:22:48 -05:00