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

382 Commits

Author SHA1 Message Date
Aditya Atluri d3559bffb4 make texture as seperate header as of now 
Change-Id: I3c65aa75f2f729eedd8c3292fa3cbc37709c1cfe


[ROCm/clr commit: 94984470d4]
 2016-11-17 11:55:29 -06:00
Aditya Atluri a997f0f074 Added i8 packed math intrinsics 
1. Added add, sub, mul packed math i8 intrinsics
2. Removed c++ packed data structures included from HCC

Change-Id: I1d109c5ce10c48b7cd3ea059478b88fc1de78499
TODO: Add better packed data structures support


[ROCm/clr commit: 603bb321ec]
 2016-11-17 01:09:12 -06:00
pensun 8ea566f2b2 Update depreciated information for threadfence_system() 
Change-Id: Id13d2f81edb51eb42b896a5c06913d59ec907c55


[ROCm/clr commit: 9aa2269d5c]
 2016-11-10 11:55:12 -06:00
Rahul Garg cd7ad3d620 hipDeviceGetByPCIBusId support for HIP/NVCC 
Change-Id: I8f82890e88d2a15f592bff192179e7d5c5362722


[ROCm/clr commit: f86c7b5b3c]
 2016-11-10 11:40:59 +05:30
Maneesh Gupta 68b4d20b26 Merge branch 'rocm-rel-1.3' into amd-develop 
Conflicts:
	include/hip/nvcc_detail/hip_runtime_api.h

Change-Id: I990a7d008da9e8dcc68250cebbc8ee6e723c7e01


[ROCm/clr commit: e3b5eef7c9]
 2016-11-10 08:56:38 +05:30
pensun 85fa855e18 fix hipProfiler* apis on NV path 
Change-Id: I6adca6151fef3a9b35348163eb6bd13f5c414172


[ROCm/clr commit: 4a8a6a4697]
 2016-11-09 15:44:01 -06:00
pensun 12a5923a2b fix for hipcallback function on NV path 
Change-Id: If80c0cfe60b1f3b1a71627b5f3f79503cba4d491


[ROCm/clr commit: e5277ab4b6]
 2016-11-09 11:33:23 -06:00
Ben Sander 74c9c6e591 Add debug for Peer APIs. Enable PeerMemcpy APIs by default. 
Change-Id: I46e39a9e7b07686a78484c1f3b5495b08e052fbb


[ROCm/clr commit: 00276d141e]
 2016-11-04 08:51:16 -05:00
pensun 8911a02b17 Update document for workaround suggestion on threadfence_system() 
Change-Id: Icccab8270604a0e578a8614b9afb3f95372f4966


[ROCm/clr commit: 212fa7033c]
 2016-11-02 16:08:27 -05:00
pensun 00ce529177 Update hipStreamNonBlocking to use cuda define on NV path 
Change-Id: I74ea09db99d602ba1c5f192b36ff7f2781176e6a


[ROCm/clr commit: 9f86e47800]
 2016-11-01 20:30:56 -05:00
Aditya Atluri 2d299543bf added inter thread data movement intrinsics 
Change-Id: I2a8a8ed49429cb7f96439bd28c4b83b5142737df


[ROCm/clr commit: f097b6ef81]
 2016-11-01 16:37:33 -05:00
Rahul Garg 5040e8bcc3 Added hipDeviceGetByPCIBusId in hip/hcc path 
Change-Id: I3cca0dc533d0281689d8a407c7da16ca1ba6a3a8


[ROCm/clr commit: 81c91f5b0b]
 2016-11-01 10:57:48 +05:30
Ben Sander f31e602346 add hip_profile.h 
Change-Id: Id43a4336db53567020584cb7842baf5c1649fd8e


[ROCm/clr commit: 9edaf0e3f7]
 2016-10-28 07:08:46 -05:00
Ben Sander 4378a14789 Add initial hipProfileStart/Stop 
And modify sample to show how to use.
Still needs some work to understand interaction with CXL.

Change-Id: I2579824d2dd7863ea23874d34f0dabb3cb305d3e


[ROCm/clr commit: 18dbafe6e8]
 2016-10-27 23:09:32 -05:00
pensun 33b6db2322 Add missing hipStream typedef for NV path 
Change-Id: I915cd14a9ff32b55b0121062d7804a7fbbdc3341


[ROCm/clr commit: dcdb7f6c68]
 2016-10-27 13:34:14 -05:00
pensun 6818eaf657 Remove extra semicolons and extra spaces in header on NV path 
Change-Id: Ib33aec2451a4e0b298d537dbb1b9df000405871b


[ROCm/clr commit: 0dbc6a1e93]
 2016-10-26 10:23:10 +05:30
pensun 6f4ae9b9c4 Remove extra semicolons and extra spaces in header on NV path 
Change-Id: Ib33aec2451a4e0b298d537dbb1b9df000405871b


[ROCm/clr commit: ee126928b1]
 2016-10-25 15:29:52 -05:00
pensun b0a039cd5e Add workaround for hipStreamAddCallback function: call stream synchronize on host and then add execute the call back function 
Change-Id: If361f8e053949904b19b9e09245d267f05e29f7b


[ROCm/clr commit: 7a0375854a]
 2016-10-22 23:59:39 -05:00
Aditya Atluri d4a090e7fb Added support for constant memory 
1. Added support for constant memory
2. Added test which uses memcpytosymbol for constant memory
3. Corrected code error on nvcc path

Change-Id: I2ab69f516832bf7a037132ac81273ea6f5107401


[ROCm/clr commit: 3a1c8f9259]
 2016-10-20 09:57:53 -05:00
Ben Sander 7fdf4828ec Add hipDeviceSchedule* support to queue wait 
Change-Id: Iffa7a356500b026f3737c3f5719ca9f62b10d855


[ROCm/clr commit: c7303d5924]
 2016-10-18 22:27:16 -05:00
Ben Sander e9997ea992 Remove some TODO items 
Change-Id: I7e9de2e43a8584f8dc9ee6d45c8ed00ca465f591


[ROCm/clr commit: 0787c41ac0]
 2016-10-18 22:27:16 -05:00
Ben Sander 1fc5bf0643 Update docs for event, review event TODO. 
Change-Id: Iec491f9f22df163f01c0af6639fcbe33c81acdcc


[ROCm/clr commit: 54b20dbe0d]
 2016-10-18 22:27:16 -05:00
Ben Sander d6ffcdb9b0 Move some internal headers from "include/hip/" to src. 
Change-Id: I7041bd5c803d9318979f4a7c1d658445c614691e


[ROCm/clr commit: 403cdf93c3]
 2016-10-18 22:27:16 -05:00
Maneesh Gupta 789d6cc42e Rename hipComplex.h -> hip_complex.h 
Change-Id: I86af4ddccc6ebb19606156b459e3065d2c979108


[ROCm/clr commit: 4a87f78fa6]
 2016-10-16 11:02:36 +05:30
Maneesh Gupta 96ce4c8e2c include headers: Update copyright header and fix line endings 
Change-Id: If2b0855f4ebf1e966edb54de5667687d154cc574


[ROCm/clr commit: a34090e9c5]
 2016-10-15 22:52:10 +05:30
Ben Sander fc7eefb5c8 Cleanup files from code review. 
- Remove some stale code
- Update docs
- Correct define for __HIP_ARCH_HAS_GLOBAL_INT64_ATOMICS__

Change-Id: Ic5e3cdb8269b1c18f6d2693700b55e08c4d0080e


[ROCm/clr commit: aa3e04cf9a]
 2016-10-15 11:51:20 -05:00
Ben Sander 57adbf2a17 Add code to use new HCC API accelerator_view::dispatch_hsa_kernel. 
Disabed by default, can enable with USE_DISPATCH_HSA_KERNEL=1

Change-Id: I7a6ba76f2bada34952ed47f5335ce695fa2faea5


[ROCm/clr commit: dcadaadb24]
 2016-10-14 23:46:29 -05:00
Maneesh Gupta 426d597cc6 Remove orphaned hip_blas.h from hcc_detail and nvcc_detail 
Change-Id: I7e2dda475b538d30942c52d86fbdb213918c630c


[ROCm/clr commit: 09b3d87767]
 2016-10-14 12:55:50 +05:30
Maneesh Gupta acae18c4ac Remove incorrect executable-bit from non-executable files 
Change-Id: Iacc434374721e01f7d75d0ab54bceabe0b337f54


[ROCm/clr commit: 2e93d2d5d2]
 2016-10-14 12:53:13 +05:30
Aditya Atluri f4bec1719f added limit enum to nvcc 
Change-Id: If9cb6b1205631da36ec18a84f736f2f2f5155885


[ROCm/clr commit: 943878eff4]
 2016-10-13 15:15:02 -05:00
Aditya Atluri 2829a64391 changed hipLimit to hipLimit_t and data type to enum 
Change-Id: I94f408cdcac4b0bb38801d58709b68e9630d44d0


[ROCm/clr commit: 34ab2a55ab]
 2016-10-13 15:13:11 -05:00
Aditya Atluri adca18892a added compiler flag for polaris 
Change-Id: Ib14c14c0618982ac7b48f5bc704c04b54ff40ed9


[ROCm/clr commit: 1970ea07f1]
 2016-10-13 14:16:48 -05:00
Ben Sander 004ca9fdfc Remove hipblas.h header - this is now hosted in the hcBlas repot. 
Change-Id: I5b3350c900741cb1aee75faf4547f2682a9ec385


[ROCm/clr commit: cfccd63b8c]
 2016-10-13 11:51:25 -05:00
Aditya Atluri 7b180aff34 Added HIP_SYMBOL macro to act as a wrapper between HCC and NVCC symbol name parameters 
Change-Id: I008d028b1e29d5a00d0e449af388216396ad2f75


[ROCm/clr commit: 2a55ae10e8]
 2016-10-13 10:31:56 -05:00
Aditya Atluri a208e9be9c added limit api support for nvcc 
Change-Id: Ib6c939e44343158a70e0de7f107d21afc0d0efba


[ROCm/clr commit: 71b98fef5e]
 2016-10-12 21:06:30 -05:00
Aditya Atluri cd32c9418e Added hipDeviceGetLimit api 
1. hipDeviceGetLimit API for HCC path is added
2. Test for hipDeviceGetLimit API is added
3. The feature added only supports querying heap size
4. Corrected indents for malloc and free device functions
5. Removed redundant data structures
6. Added g_heap_malloc_size to store the heap size

Change-Id: If48d1b0ce9270e994f1c542cc283ddbb14746bbb


[ROCm/clr commit: e5325a1ab4]
 2016-10-12 19:58:48 -05:00
Aditya Atluri 9536444ee5 Added copyright for headers 
Change-Id: I35843d8d3b6acd9553ce00150868e15e2baee1da


[ROCm/clr commit: e8029e4b5f]
 2016-10-12 19:12:35 -05:00
Aditya Atluri caa6a298e7 added malloc and free device functions 
1. Added malloc and free device functions
2. Added test which check malloc and free functions
TODO: Need to add support for multiple device. Works only on one device (multi device support id NOT available).

Change-Id: Id11fc36463915d6ad46c264d5a20c8feb2d2c17c


[ROCm/clr commit: 2918ff273d]
 2016-10-12 19:08:34 -05:00
Aditya Atluri 84476c5e33 changed memcpy and memset device functions 
Change-Id: Ia7f450536a75fad4fe13c7fcf5e9e7a9b5450f52


[ROCm/clr commit: ff59ea76f1]
 2016-10-11 17:43:15 -05:00
Aditya Atluri ac89997057 changed hipTestDeviceSymbol test to compile for both nvcc and hcc path 
Change-Id: I041770ad59d4f88d0c8d27d90cdc8a799935ada1


[ROCm/clr commit: 8e8939d775]
 2016-10-11 13:50:31 -05:00
Aditya Atluri 41a18e4a01 added hipMemcpySymbol feature to nvcc path 
Change-Id: I78d45036083fba62d2b2e4e58f9c72cb4e6eb54f


[ROCm/clr commit: 5274244f7e]
 2016-10-11 13:34:54 -05:00
Aditya Atluri 41077d99af added more changes to memcpytosymbol 
1. Refactored code to use HCC internal APIs rather than HCC copy APIs
2. Added hipMemcpyToSymbolAsync
3. Added test for hipMemcpyToSymbolAsync
4. Added new error hipErrorInvalidSymbol

Change-Id: I0e359b2d0ff5d682bbccdf9c2923e16b35e39497


[ROCm/clr commit: 0bf811b875]
 2016-10-11 13:29:46 -05:00
Aditya Atluri 68b3ae7fce Added feature for memcpy to Symbol 
1. Currently works only for __attribute__((addrspace(1))
2. Need to pass in string for name of the variable
3. Added test to check functionality

Change-Id: I4c3cc1bf151cb5423e4aef59fcc4ad5693b31641


[ROCm/clr commit: 89b576da65]
 2016-10-11 12:09:58 -05:00
Aditya Atluri df5370763a added threadfence feature for hcc 
1. Added feature for __threadfence and __threadfence_block
2. Added feature for using LLVM IR files directly while compilation
3. Added test for threadfence and threadfence_block

Change-Id: Ib7e5d89b4cca1a135952b317e5809cd05b56a3c9


[ROCm/clr commit: 09c9953649]
 2016-10-10 15:29:50 -05:00
Maneesh Gupta 4cef1070b2 Add back deprecated hipHostAlloc, hipMallocHost, hipFreeHost 
Change-Id: Ib8494078c852b07e1958c3acc21fa1866542122c


[ROCm/clr commit: b59659f0c7]
 2016-10-09 16:30:46 +05:30
Elias Konstantinidis c7da2fe434 Added support for __mul24 and __umul24 
[ROCm/clr commit: adc763f440]
 2016-10-06 09:29:36 +05:30
Maneesh Gupta 46feb7dcf2 Move include/* to include/hip/* 
Change-Id: I7a7b2839b4df59c7a4c503550f99fdc9e45c0f54


[ROCm/clr commit: bbfc08f419]
 2016-10-04 22:17:18 +05:30
Ben Sander c47374f479 Fix hipMemSetAsync compilation, bounds check on name copy 
[ROCm/clr commit: 48849feba3]
 2016-10-03 19:05:19 -05:00
Aditya Atluri 21ef342e65 Stream fix on nvcc hipMemsetAsync 
Change-Id: Ia0eb81dff0f422af55d93b4635d42e9aa6921377


[ROCm/clr commit: 3edff7dd3b]
 2016-10-03 12:38:41 -05:00
Ben Sander 77014b3165 disable DB_SHOW_TID 
Change-Id: Ia415437e8ba9903de149997380f61f1272488642


[ROCm/clr commit: 0bcb54be35]
 2016-10-02 05:56:38 -05:00