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

582 Commits

Author SHA1 Message Date
Maneesh Gupta 281c543bc3 Make elfio headers private 
Change-Id: I3ba174bb46e84a75380207d93a0da6fe3703689e
 2017-10-23 10:24:36 +05:30
Alex Voicu 2de3ab422f Merge remote-tracking branch 'origin/master' into feature_support_globals_for_module_api 2017-10-09 13:28:13 +01:00
Alex Voicu 582779c6c6 This adds cursory support for globals to the HIP module loading API. The 
style is purposefully alien so as to signal that HIP experts should turn
it into HIP worthy code as soon as possible.
 2017-10-09 13:27:11 +01:00
Maneesh Gupta 132316fecf Merge pull request #194 from bensander/fix_genco_math_path 
Fix math ordering for --genco mode.
 2017-10-03 16:17:34 +05:30
Ben Sander 2e9b78c274 Fix math ordering for --genco mode. 2017-10-02 21:52:16 +00:00
Rahul Garg 71a5a0cb42 Fixed review comment 2017-10-02 17:29:08 +05:30
Rahul Garg 79a943e654 Fixed review comments 2017-10-02 10:57:25 +05:30
Rahul Garg d92cfa44d2 Fixed build issue 2017-10-02 10:40:01 +05:30
Rahul Garg e6725e2b7a Fix texture support on HIP/NVCC path 2017-10-02 10:40:01 +05:30
Siu Chi Chan bf6a3f4294 ensure the condition is evaluated before applying the negation operator 2017-09-20 01:38:28 -04:00
Maneesh Gupta 01163d327b Merge pull request #155 from wsttiger/master 
Modify hip headers such that they are more compatible with strict C compiler
 2017-09-15 10:49:55 +05:30
Maneesh Gupta 846b0555b9 Fix typo in nvcc_detail/hip_runtime_api.h 2017-09-14 16:19:57 +05:30
Maneesh Gupta 096caca840 Merge pull request #175 from gargrahul/assert_support 
Device side assert support
 2017-09-14 16:08:00 +05:30
sriharikarnam f6fda276ce Add hipDevice[Get/Set]SharedMemConfig API on nvcc details 2017-09-14 16:03:19 +05:30
Rahul Garg 9dcf2ad751 Device side assert support 2017-09-07 20:45:27 +05:30
Ben Sander a6d1778fff Update docs. 
- Review unsupported comments and refresh.
- Review experimental tag in API.
 2017-08-28 15:44:38 -05:00
wsttiger 8302138d57 Modify header such that it's compatible with strict C compiler 2017-08-15 13:23:09 -05:00
wsttiger 7933b3292d Add missing CUDA tags 2017-08-15 13:22:20 -05:00
Siu Chi Chan b6e22b5c93 implement __threadfence_system 2017-08-02 08:50:18 +00:00
Ben Sander 702651fc85 Merge pull request #100 from weixingzhang/texture 
HIP Texture Support
 2017-07-26 19:28:15 -05:00
Maneesh Gupta 1bd1c6bea8 Renable frexp(f) device math function 
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395
 2017-07-20 14:41:30 +05:30
Weixing Zhang ccbd3b13fc HIP Texture Support 2017-07-17 15:16:12 -04:00
Wen-Heng (Jack) Chung 0237aeab06 Remove explicit address spaces declarations 2017-07-07 12:46:29 -05:00
Ben Sander 18660be8ce Add hipdbPrintMem - wrapper for hcc memory tracker. 2017-07-03 15:05:30 -05:00
Rahul Garg cbc98cc098 Fixed build error in hipDeviceGetByPCIBusId 
Change-Id: I33be362910c4c5dca7435fb9c41f427b54f0e9a7
 2017-07-01 07:56:30 +05:30
Ben Sander 5e5b017b0d Refactor hip_hcc. 
Don't require setting __HIP_PLATFORM_HCC__ ; Instead check if compiler is HCC.
The functions here use HCC-specific functionality so only work with HCC.
ANd they work regardless of the __HIP_PLATFORM_HCC__ setting so don't
require that.

Also remove the "hcc_detail" extra hierarchy level for hip_hcc.h as
it is not necessary.  Remove hcc_detail/hip_hcc.h.
 2017-06-30 08:26:15 -05:00
Rahul Garg 467a2ba014 Fixed hipDeviceGetByPCIBusId 
Change-Id: Ia36bb9425671ef7659541c9aeedae4098456a31b
 2017-06-30 10:11:41 +05:30
Rahul Garg 38d48b5cf0 Fixed hipDeviceGetPCIBusId for HIP/NVCC 
Change-Id: I662efa148257a710f09002850b41d57bef00dff3
 2017-06-29 00:13:02 +05:30
Rahul Garg a7c727f352 Fixed hipDeviceGetPCIBusId for HIP/HCC 
Change-Id: I3688fa2476e1baada2d3c5fc3735cec3f15a1e21
 2017-06-28 23:48:27 +05:30
Sun, Peng 3d2a729580 Remove some warning debug info and add weak attribute back to GGL __global__ define 
Change-Id: I2021b107dda697b1262d44fa1506465e94a3916b
 2017-06-27 14:15:16 -05:00
Aditya Atluri 3043766899 fixed default args for symbol memcpy apis 
Change-Id: Ie0b63f8b9c5535eb3946bd6af3f30fe71a015244
 2017-06-23 19:05:44 -05:00
Ben Sander 42882ddf9c Clean up old USE_* and RELEASE.md notes. 2017-06-23 18:05:30 -05:00
Rahul Garg 0fd6b59e22 Added device side abort function in HIP/NVCC 
Change-Id: I6ae35a72a8b9c34852619f02da1a046c8d3b2ed3
 2017-06-20 09:38:56 +05:30
Rahul Garg d9935cd089 Abort device function in HIP/HCC, need new HCC 
Change-Id: I4195ab75e9b7b48c8b8128d6925ddc0fa5e9e009
 2017-06-18 12:31:31 +05:30
Aditya Atluri 34e14bb02d removed bad copy constructor 
Change-Id: I661991d9d43941a61848b0b8e9879c0bfa811b40
 2017-06-16 09:02:26 -05:00
Sun, Peng 9bce2af76f Additional GGL make_kernel_functor_* macros, contributed by Alex 
Change-Id: I01aabb7d2b5418fcefb1bbf78eb5d1888dbc5c96
 2017-06-14 11:10:52 -05:00
Sun, Peng 682dda4418 Fix error related to undefined reference of __get_dynamicgroupbaseptr(). 
Change-Id: I14951e1725e35dd5f5e53805f81cdb58661f59f2
 2017-06-08 19:24:32 -05:00
Sun, Peng 5450021f93 Add clang version guard so the hip_fp16.h header won't be picked up by gcc 
Change-Id: Ia21335a455bc93210901b44bc8c76a7f4a385b55
 2017-06-08 19:24:32 -05:00
Sun, Peng 3b6a863eef Improve HIP kernel names, attributes and codegen, contributed by Alex Voicu 
Change-Id: I2cafbdc5a98e26c7f4fad84739c915e7dc09993c
 2017-06-05 11:39:00 -05:00
Ben Sander 823281dcba Fix HIP_SYNC_NULL_STREAM=0 mode. 
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow
 2017-06-05 08:50:22 -05:00
Aditya Atluri fdcc223842 added half data type and vector destructors 
1. Added half data types to hip_fp16.h
2. Added destructor to vector data types

Change-Id: Id5ae76a663bb90a4bde2839ec79c58fbaee5072f
 2017-06-02 11:19:33 -05:00
Evgeny Mankov 463c026976 [HIP] [HIPIFY] CUDA Driver API 8.0.44 JIT options support. 2017-05-31 18:55:29 +03:00
Ben Sander 942ec0eff8 Add event controls for release fences. 
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
   (remove hipEventDisableSystemRelease)

Update test for new functionality.
 2017-05-27 16:02:34 -05:00
Ben Sander 8dc968f036 Updates so hip compiles on CUDA. 2017-05-27 15:55:07 -05:00
Ben Sander dda70ae514 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.
 2017-05-24 00:48:10 -05:00
pensun 2523f8a492 fix GGL helper header file, reorder for C++17 
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213
 2017-05-22 08:52:43 -05:00
Evgeny Mankov ae9f14ef9c [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.
 2017-05-19 17:22:14 +03:00
Aditya Atluri 0433a2e608 fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm 
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd
 2017-05-18 10:51:07 -05:00
Aditya Atluri 93fa174900 changed vector types to make sure it generate proper llvm vector types 
Change-Id: I6c4616dae137dc4eac35e5827dc5b7f3251e0247
 2017-05-16 21:35:40 -05:00
Ben Sander 8bc6ee5932 Add initial HIP_SYNC_NULL_STREAM=0 mode. 
This eliminates host-synchronization for null stream.  Instead, the
null-stream uses GPU-side events to wait for other streams.
Default is OFF pending additional testing.

Add enhanced null-stream test.

Also refine HIP_TRACE_API.
 2017-05-16 19:04:25 -05:00