Maneesh Gupta
236413158d
Merge pull request #482 from ROCm-Developer-Tools/feature_clean_up_hip_math
...
Switch to using ROCDL directly, as opposed to via HC. Add missing bits.
[ROCm/clr commit: cb642f14ab ]
2018-06-06 16:07:22 +05:30
Maneesh Gupta
e34247ca19
Merge pull request #497 from gargrahul/fix_memcpy3d_fastpath
...
Fix hipMemcpy3D for fast path
[ROCm/clr commit: 53037472ff ]
2018-06-06 14:44:02 +05:30
Maneesh Gupta
7398a6eec1
Merge pull request #492 from gargrahul/fix_depth_3d_alloc
...
Fix depth value for 3D allocations
[ROCm/clr commit: 28c5b15d88 ]
2018-06-06 14:41:23 +05:30
Maneesh Gupta
cb5549ac34
Merge pull request #491 from scchan/fix_wait
...
callback handling: don't need to wait for the thread to become ready
[ROCm/clr commit: f7c49dde38 ]
2018-06-06 14:38:25 +05:30
Rahul Garg
914a0aaf9c
Fix hipMemcpy3D for fast path
...
[ROCm/clr commit: 163d4a5b03 ]
2018-06-05 18:54:33 +05:30
Siu Chi Chan
8cfbffb82b
remove the _ready flag in ihipStreamCallback_t and the mutex that protects it.
...
[ROCm/clr commit: 0d719c514f ]
2018-06-04 17:29:04 -04:00
Rahul Garg
3a6e8aadbd
Fix depth value for 3D allocations
...
[ROCm/clr commit: fa6ce7a724 ]
2018-06-04 18:00:22 +05:30
Siu Chi Chan
07d06ef156
callback handler: don't need to wait for the thread to become ready
...
[ROCm/clr commit: e21e6ed3a0 ]
2018-06-02 17:55:37 -04:00
Alex Voicu
193e41fdde
Remove vestigial implementations.
...
[ROCm/clr commit: 68a0dd826d ]
2018-06-02 11:37:08 +01:00
Rahul Garg
065f0d8d8c
Add integrated device property
...
[ROCm/clr commit: 94f086e9cd ]
2018-06-02 13:11:16 +05:30
Alex Voicu
130e9d409e
Re-sync with upstream.
...
[ROCm/clr commit: f2d7f112ab ]
2018-06-01 15:49:05 +01:00
Maneesh Gupta
73cbb7bb7b
Merge pull request #484 from gargrahul/fix_malloc_hiphostreg
...
Fix memcpy2D for malloc+ hostRegister
[ROCm/clr commit: 095d4dd91e ]
2018-06-01 16:53:25 +05:30
Maneesh Gupta
125f6201c8
Merge pull request #466 from ROCm-Developer-Tools/feature_use_Float16
...
Feature use _Float16 and match CUDA __half behaviour.
[ROCm/clr commit: 8ecb3eeb55 ]
2018-06-01 13:50:12 +05:30
Alex Voicu
a9cabfc8df
Re-sync with upstream. Add integer abs.
...
[ROCm/clr commit: e03ca1a72e ]
2018-05-31 16:38:00 +01:00
Rahul Garg
84cb355df6
Fix memcpy2D for malloc+ hostRegister
...
[ROCm/clr commit: a3609eaf61 ]
2018-05-31 13:14:27 +05:30
Alex Voicu
2924783ee4
Switch to using ROCDL directly, as opposed to via HC. Add missing bits.
...
[ROCm/clr commit: 14e6a04387 ]
2018-05-31 03:17:26 +01:00
Maneesh Gupta
b074d762fa
Merge pull request #472 from Jorghi12/patch-3
...
Adding double/long int signatures for abs
[ROCm/clr commit: 3327a9a2de ]
2018-05-30 08:32:14 +05:30
Jorghi12
9b43fd84d0
Update math_functions.cpp
...
CUDA also has a function named labs.
[ROCm/clr commit: 61ff40a1cf ]
2018-05-26 16:21:14 -04:00
Jorghi12
fbbaedfdea
Adding double/long int signatures for abs
...
Adding overloads for abs that are found in cuda's math_functions.
[ROCm/clr commit: 13f37d550f ]
2018-05-26 00:40:14 -04:00
Rahul Garg
0ab5c9d6f1
Use 64x4 grid dims
...
[ROCm/clr commit: 27e0566c3a ]
2018-05-24 23:51:52 +05:30
Rahul Garg
439655d213
Clean up and fix remaining bytes copy
...
[ROCm/clr commit: aed2653857 ]
2018-05-24 23:30:27 +05:30
Alex Voicu
a231cd5604
Remove vestigial inline LLVMIR.
...
[ROCm/clr commit: f2a86f3e1c ]
2018-05-24 12:46:14 +01:00
Rahul Garg
4fc64ff4c5
Fix memcpy2d kernel dims
...
[ROCm/clr commit: 53a7c61e9b ]
2018-05-24 17:00:12 +05:30
Rahul Garg
4e52a634a1
Correct remaining bytes in copy 2d kernel
...
[ROCm/clr commit: 96b4618d26 ]
2018-05-24 08:27:24 +05:30
Alex Voicu
2b16b4e31b
Missing commit.
...
[ROCm/clr commit: ecefdd6541 ]
2018-05-23 17:57:47 +01:00
Rahul Garg
432467d88b
Optimize memcpy2D kernel use
...
[ROCm/clr commit: 2c3d1498d4 ]
2018-05-23 14:43:47 +05:30
Maneesh Gupta
335dad2feb
Merge pull request #464 from gargrahul/fix_memcpy2d_pinned_mem_case
...
Fixed memcpy2D for pinned memory case using 2D kernel
[ROCm/clr commit: 7042fe6067 ]
2018-05-22 10:42:28 +05:30
Maneesh Gupta
e72516bd2f
Merge pull request #445 from ROCm-Developer-Tools/feature_func_attributes
...
Add support for the hipFuncGetAttributes interface.
[ROCm/clr commit: 85342d73b5 ]
2018-05-22 09:37:41 +05:30
Rahul Garg
54497d1e2b
Fixed memcpy2D for pinned memory case using 2D kernel
...
[ROCm/clr commit: 40fb44dbe6 ]
2018-05-21 22:14:45 +05:30
Maneesh Gupta
efe6b5e4a0
hipMemcpy returns success if sizeBytes is 0.
...
Fixes SWDEV-153754 & SWDEV-154178.
[ROCm/clr commit: 66d05e6fc3 ]
2018-05-21 15:38:44 +05:30
Maneesh Gupta
32911a3b9c
Merge pull request #455 from ROCm-Developer-Tools/magic
...
Change HIP fat binary magic number
[ROCm/clr commit: cfb7be414b ]
2018-05-21 09:52:03 +05:30
Alex Voicu
677e945726
Update hip_module.cpp
...
Typo.
[ROCm/clr commit: 43fca684c8 ]
2018-05-18 17:50:45 +01:00
Rahul Garg
8575112052
Fix for memcpy2DAsync for pinned host memory case
...
[ROCm/clr commit: 4f5bdb071c ]
2018-05-18 21:09:50 +05:30
Maneesh Gupta
106f3f591e
Merge pull request #433 from gargrahul/add_hipmemset3d
...
Added hipMemset3D
[ROCm/clr commit: 1c93e11cdf ]
2018-05-18 14:54:15 +05:30
Maneesh Gupta
4eb7565f85
Merge pull request #448 from 949f45ac/master
...
Provide correct __mul64hi and __umul64hi builtins, using code from ROCm-Device-Libs
[ROCm/clr commit: bb1f53ac44 ]
2018-05-18 13:18:16 +05:30
Yaxun (Sam) Liu
3d75c87c26
Change HIP fat binary magic number
...
[ROCm/clr commit: 2f9bce3652 ]
2018-05-17 17:04:51 -04:00
949f45ac
901ab53c37
Reinstate accidentally deleted uchar2Holder
...
[ROCm/clr commit: 7bf8402d1d ]
2018-05-17 10:55:45 +02:00
Rahul Garg
84089036b0
Fixed hipMemcpy2D to handle 1D memcpy case
...
[ROCm/clr commit: 8413fb51e1 ]
2018-05-16 11:07:10 +05:30
Alex Voicu
5a9d5a931b
Update hip_module.cpp
...
[ROCm/clr commit: 40a22d235e ]
2018-05-14 17:15:36 +01:00
949f45ac
c819e2ee01
Provide correct __mul64hi and __umul64hi builtins, using code from ROCm-Device-Libs
...
[ROCm/clr commit: 9210263727 ]
2018-05-14 08:34:56 +02:00
Alex Voicu
2973f68465
Don't use magic constants, they're evil.
...
Also clarify that the register count cannot be queried at the moment.
[ROCm/clr commit: eded014abc ]
2018-05-11 11:31:46 +01:00
Alex Voicu
4e6996282d
Add support for the hipFuncGetAttributes interface.
...
[ROCm/clr commit: bf9529aaa8 ]
2018-05-11 03:35:10 +01:00
Rahul Garg
a7be5be448
Added hipMemset3D
...
[ROCm/clr commit: 78568435da ]
2018-05-07 10:24:30 +05:30
Lakhan Singh
6278830c1a
Null checks added for hipmallocpitch and hipmemcpy apis
...
[ROCm/clr commit: 12d8a47c0c ]
2018-05-03 09:27:50 +05:30
Rahul Garg
6f05c37cde
Fix texture 3D for HIP/NVCC
...
[ROCm/clr commit: 1d76c48e3d ]
2018-05-02 11:56:37 +05:30
Maneesh Gupta
9ac65ca55c
Merge pull request #415 from deven-amd/master
...
Checkin to fix bugs in math functions.
[ROCm/clr commit: af0c227df4 ]
2018-05-01 12:29:03 +05:30
Deven Desai
13ab5368d0
Checkin to fix bugs in math functions.
...
This change fixes the following bugs that were discovered while debuggnig TF unit test failures (cwise_ops_test)
1. __hisinf and __hisnan routines
Both had incorrect implementations.
2. abs
A "long long" (64bit int) version was missing, resulting in the 32bit version being used for 64bit ints (which resulted in incorrect results, when the value passed in was outside the 32bit int range)
3. lgamma
We seemed to have a custom version for the 'double' datatype (which was giving incorrect results). Replaced it with a call to the 'double' version of the underlying 'hc::precision_math::lgamma'
[ROCm/clr commit: 65a90c55e7 ]
2018-04-24 18:10:07 +00:00
Lakhan Singh
06dd83f7f1
SWDEV-141024
...
[ROCm/clr commit: 74faa61d52 ]
2018-04-20 17:40:00 +05:30
Rahul Garg
39a19cc9e8
Added hipMemset2DAsync support
...
[ROCm/clr commit: fcc0866681 ]
2018-04-17 18:27:27 +05:30
Maneesh Gupta
295cd826d9
Merge pull request #400 from gargrahul/hipModule_cleanup
...
hip_module code cleanup
[ROCm/clr commit: 72ff4c5cc4 ]
2018-04-17 09:00:15 +05:30