AI/rocm-systems
2
0
Fork 0
Code Issues Pull-Requests Actions Pakete Projekte Releases Wiki Aktivität
1.617 Commits 3 Branches 0 Tags
05be936fd6ee2fa45fbab68cc70765782e7af8fe
Commit graph

1617 Commits

Dieser Branch
Dieser Branch
Alle Branches
Autor SHA1 Nachricht Datum
Evgeny Mankov 05be936fd6 [HIPIFY] LLVM 3.9 support 
3.8 and 3.9 are both supported. 3.8 is stable, 3.9 needs more testing.
 2017-05-05 21:28:02 +03:00
Rahul Garg 1cb51d614e hipMemcpy2DAsync for HIP/NVCC 
Change-Id: I46f0057fef49bdaaac41c1df80c3e27432b8f376
 2017-05-04 06:47:55 +05:30
Evgeny Mankov 9b65358c68 [HIPIFY] CUDA RT memcpy functions update. 
cudaMemcpyFromSymbol -> hipMemcpyFromSymbol
cudaMemcpyFromSymbolAsync -> hipMemcpyFromSymbolAsync
cudaMemcpy2DAsync -> hipMemcpy2DAsync
 2017-05-03 23:05:44 +03:00
Evgeny Mankov 1269897606 [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
 2017-05-03 22:45:56 +03:00
Evgeny Mankov 70c94d7b83 [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.
 2017-05-03 21:59:48 +03:00
Rahul Garg ec27c695c4 Added support for hipMemcpy2DAsync in HIP/HCC 
Change-Id: Ia4a8306f2dc1e33a81a7195ec29aef652fcccc4b
 2017-05-03 22:29:12 +05:30
Evgeny Mankov c7958cbb8b [HIPIFY] Rename enumConstantDecl -> enumDecl 
Reason: not to mix up with clang's enumConstantDecl, used for enum DeclRefExpr (enum constant).
 2017-04-28 21:59:33 +03:00
Evgeny Mankov eddd021996 * [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).
 2017-04-28 21:45:36 +03:00
Evgeny Mankov 3d88932c8d [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.
 2017-04-28 21:03:03 +03:00
Aditya Atluri a5cb2d40ec fixed hipFuncSetCacheConfig on rocm path 
Change-Id: I937a3afbf115edc94a753a0beb2230ed60a6f021
 2017-04-28 11:53:11 -05:00
Aditya Atluri ab2eb420e2 fixed fast math expf and exp10f 
Change-Id: I73963220f902efebb0a7404c5f8966dffb4c35ca
 2017-04-26 19:01:10 -05:00
Aditya Atluri fc6248ce82 added hipFuncSetCacheConfig API for nvcc path 
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d
 2017-04-26 18:56:57 -05:00
Maneesh Gupta ff454e4b8e Merge branch 'amd-master' into amd-develop 2017-04-26 23:55:13 +05:30
Sun, Peng 54561c8af3 fix hip_complex.h header on NV path 
Change-Id: Ia95d003ca1b284bab1c76723050e6b3b89178f65
 2017-04-25 00:15:20 -05:00
Ben Sander cd93a2f229 Add host offset checking 2017-04-24 22:30:54 -05:00
Ben Sander b7b17c3841 Refactor hipHostRegister test. 
- Add more testing for offsets.
- Parse cmdline options and use --tests.
 2017-04-24 22:30:54 -05:00
Ben Sander 8ba993e36c Refactor hipHostRegister to cover misaligned cases. 2017-04-24 22:30:54 -05:00
Ben Sander 5a52b79782 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.
 2017-04-24 22:30:54 -05:00
Ben Sander ab410add5c Add test for non-page-aligned mem copies. 2017-04-24 22:30:54 -05:00
Ben Sander c5d89d9e7f Add corrected test for offsets 2017-04-24 22:30:54 -05:00
Ben Sander 2bc0a6030e Refactor hipMemcpy test to share mem alloc for multiple copies. 2017-04-24 22:30:54 -05:00
Ben Sander dc001ef9b4 Add negative testing for memory full condition. 2017-04-24 22:30:54 -05:00
Ben Sander 9e41e3c6e2 Fix hip debug for case where copyAgent is null (host-to-host) 2017-04-24 22:30:54 -05:00
Ben Sander 59df70662a Fix hipMalloc to return error code if allocation fails. 2017-04-24 22:30:54 -05:00
Aditya Atluri 59ab3659ee fixed build issues with hipPointerGetAttributes 
Change-Id: I3f5fbc05bdaef720884ba949075928752a070377
 2017-04-24 15:31:07 -05:00
Aditya Atluri 72bcfa438b changed arguments for hipPointerGetAttributes 
Change-Id: Ia7a7c4722c1f7d0a23f0e5cc3dd6dea6c01c1fd8
 2017-04-24 15:24:16 -05:00
Maneesh Gupta 88fb807af0 Merge branch 'amd-develop' into amd-master 
Change-Id: I312fb9d1181733ef5160d1e993e2ae57ced0f6b3
 2017-04-24 08:51:03 +05:30
Maneesh Gupta 3a519ee9e5 Updated release notes 
Change-Id: Ia98aff420ea9d488924dce8fe9168cec9da301ab
 2017-04-24 08:48:35 +05:30
James Edwards 4869bf5a7c Specify full path of hip libraries in link file. 
Change-Id: I49b788f3489e7abff6b11006ff97fdfca4e5942c
 2017-04-22 15:54:14 -05:00
James Edwards 36353a560f Properly link hip cmake file into top level lib directory. 
Change-Id: I2113a86ca6985f34fd0cfb091abdbce0f632cfc2
 2017-04-21 22:34:26 -05:00
Evgeny Mankov 080dd2e0d3 [HIPIFY] [DOC] Readme.md update: Ubuntu 16.04 support 2017-04-22 01:01:31 +03:00
Evgeny Mankov 3c1dd246d6 [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.
 2017-04-21 21:46:30 +03:00
Ben Sander 6d5ac3fbac Fix compilation error with nvcc (c++ nullptr) 2017-04-21 09:01:34 -05:00
Sun, Peng f4287a29b2 add support of hipLaunchKernelGGL on NV path 
Change-Id: I0aeafd80c2181873be385d985f1d8ed86a98d136
 2017-04-19 11:00:25 -05:00
Sun, Peng fa15ee3ccd fix broken header in NV path 
Change-Id: Ia3aff2a89d9ba49547f51ce03a3304dfab58ba25
 2017-04-19 10:47:40 -05:00
James Edwards 1b6d08ada0 Fix RPM HIP packages from specifying /opt 
Change-Id: Iec3c3b81eef4c8888d425eefc80b12488a8d20a1
 2017-04-19 12:35:42 +05:30
James Edwards 7699aeb3d3 Fix RPM HIP packages from specifying /opt 
Change-Id: Iec3c3b81eef4c8888d425eefc80b12488a8d20a1
 2017-04-17 23:58:34 -05:00
Maneesh Gupta 486716a400 FindHIP: Apply remove_item on non-empty lists only 
Change-Id: Ib7fcb992d7e1bb679d4d86676fe3d980ba204815
 2017-04-18 10:21:20 +05:30
Ben Sander 4f363df159 Update bugs - Add CreateKernel, new signature for static kerns. 2017-04-16 14:22:48 -05:00
Maneesh Gupta 0a9feb4f61 FindHIP: Handle remove_item from empty lists 
Change-Id: I6adf31b32edeae9e8454b1a2528064cf3985fca1
 2017-04-13 14:41:11 +05:30
Maneesh Gupta 3a56e5c09b Merge branch 'amd-develop' into amd-master 
Change-Id: I05572d2b32f1df70b54e2efeb32c8a4d8055912d
 2017-04-13 12:39:36 +05:30
Maneesh Gupta bfa08cd49a Do not rebuild cmake cache by default 
Change-Id: Ie21e99beaa3465b54b5a6a77439c455f34de98b3
 2017-04-13 12:38:38 +05:30
Maneesh Gupta 83097e9da4 dtests should ignore HIP_PATH env var 
Change-Id: I27b1cdab6e6b799987dad3ce97b56c764b1b8867
 2017-04-13 12:12:04 +05:30
Maneesh Gupta 7bb378bd4d Add hip-config.cmake to hip_hcc package 
Due to the way hip packages are generated, for the purpose of
packaging hip-targets*.cmake are not generated at build time.
However hip-config*.cmake are generated at build time.
This will be fixed in future.

Change-Id: I5d79bc58a4f7a324ae06457130d8372ffe403830
 2017-04-13 10:34:33 +05:30
Ben Sander 22f3b91cad Add integer abs (initial implementation, can be optimized with OCML) 
Change-Id: I1f568c8c0e2333af1fda4c313dc48ea0c5b6ab00
 2017-04-11 01:16:28 +00:00
Ben Sander 310c130fc6 Doc update for Serialization. 
Describe workaround for partial specialization
 2017-04-10 19:45:18 -05:00
Sun, Peng 71447dacad Fix ifndef guard in hip_fp16.h 
Change-Id: I0215556e7aa98a74e8a984e4de3fb6e8cafdfb24
 2017-04-10 11:17:05 -05:00
Sun, Peng 2848d7a222 add math.h to cover sqrtf function 
Change-Id: Ia37752710cea4ca77e0a4e61f8e69a0355d9488d
 2017-04-10 08:53:12 -05:00
Sun, Peng a9fd0d4e0d Update the define of __global__ for GGL 
Change-Id: I563bb2a132403bcbe9e9f279b55406cf0255af7d
 2017-04-07 16:39:33 -05:00
Sun, Peng a5ca430e5c Add more operator overloading for float2 type, contributed by Aditya 
Change-Id: If1ab7fb24d64bb5304142aed0951c9bd5ad47d20
 2017-04-07 14:17:41 -05:00