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

390 Commits

Author SHA1 Message Date
Aditya Atluri a7bb6239ab fixed texture header on nvcc 
Change-Id: Ibe19f94be5edf972b6b51dea263e1088b6c60c1d


[ROCm/clr commit: 2ded0ce302]
 2016-11-21 13:53:28 -06:00
Aditya Atluri 72ff879c0a removed warnings in macros 
Change-Id: I992b11f6aee2bab09f46885a2d12234aa6814cc5


[ROCm/clr commit: fef766df88]
 2016-11-21 09:04:36 -06:00
Aditya Atluri 59c423b36a fixed compilation bugs 
1. Texture functions are now compiling fine
2. Fixed hipFuncCache to hipFuncCache_t

Change-Id: I8f815887e4de43ee115bbaff249905b236541c39


[ROCm/clr commit: 2611de2477]
 2016-11-21 08:56:30 -06:00
Aditya Atluri df27127960 Fixed hipDeviceGetCacheConfig on nvcc path 
1. Changed test macro to emit line numbers
2. Added getcacheconfig api test for nvcc path
3. Fixed hipFuncCache_t data type

TODO: With this commit, right now there are 2 func cache datatypes
a. hipFuncCache_t for runtime API
b. hipFuncCache for driver API

Map these to a single data type

Change-Id: Ia47c9f5d7c2633638051bf17b1103048a1ede973


[ROCm/clr commit: b3c16ea7b5]
 2016-11-20 12:18:08 -06:00
Aditya Atluri 76fbc233af added copy right to new header 
Change-Id: I16e1d02194551e4b20019bcb6850a3f84882ef18


[ROCm/clr commit: cc829f04c5]
 2016-11-19 23:02:56 -06:00
Aditya Atluri 21470101c7 added tests to check nvcc runtime api output 
Change-Id: Ifdd39b5d0a6a58d20a8e9745e59dd82d50a90e2f


[ROCm/clr commit: 6692ee09d7]
 2016-11-19 21:36:28 -06:00
Maneesh Gupta b13556367d Refactor for building HIP as dynamic library 
Change-Id: I65a3d9d589c4fdbbdcf1611e5427224253be8260


[ROCm/clr commit: 2195e3c37d]
 2016-11-18 14:33:20 +05:30
Aditya Atluri cc573d140d moved runtime macros to runtime_api.h 
Change-Id: Ib47e449328e8e6ec55d1b6ee19899de4b591ea8e


[ROCm/clr commit: 3b1f0e903c]
 2016-11-17 14:19:18 -06:00
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