Oak Zeng
c3dcb0a7bb
Revert "Revert "More cleanup of fmm.c""
...
This reverts commit 5b0ba9550c .
Change-Id: I31afe4889794df8cf1e96f5f18771bed75a213d9
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com >
[ROCm/ROCR-Runtime commit: c2dc301792 ]
2017-12-04 15:48:11 -05:00
Oak Zeng
786e470241
Revert "Revert "Cleanup fmm.c""
...
This reverts commit f7689d4fef ,
Plus a bug fix to patch "Cleanup fmm.c":
Call id_in_array with correct parameter. The third parameter
of id_in_array is size in byte of the array, not the number
of array items. Call it correctly.
Change-Id: I72d8e2fcc0df32af76c72967386e92c1be18c159
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com >
2017-12-04 15:48:11 -05:00
Oak Zeng
6c763e99fe
Revert "Revert "Cleanup fmm.c""
...
This reverts commit dbd9a8736c ,
Plus a bug fix to patch "Cleanup fmm.c":
Call id_in_array with correct parameter. The third parameter
of id_in_array is size in byte of the array, not the number
of array items. Call it correctly.
Change-Id: I72d8e2fcc0df32af76c72967386e92c1be18c159
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com >
[ROCm/ROCR-Runtime commit: 786e470241 ]
2017-12-04 15:48:11 -05:00
Felix Kuehling
587d4f4bdf
Rename fmm_allocate_memory_in_device
...
to fmm_allocate_memory_object. This function name was confusingly
similar to fmm_allocate_device and __fmm_allocate_device. The new name
reflects its function better: allocate the VM object and the kernel
mode buffer object.
Change-Id: I6604d228004b4d41e871d4de784786823608b5d6
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com >
2017-12-04 10:23:55 -05:00
Felix Kuehling
cfd86f5b7e
Rename fmm_allocate_memory_in_device
...
to fmm_allocate_memory_object. This function name was confusingly
similar to fmm_allocate_device and __fmm_allocate_device. The new name
reflects its function better: allocate the VM object and the kernel
mode buffer object.
Change-Id: I6604d228004b4d41e871d4de784786823608b5d6
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com >
[ROCm/ROCR-Runtime commit: 587d4f4bdf ]
2017-12-04 10:23:55 -05:00
Jenkins
7ca3b9472f
Merge 'master' into 'amd-master'
...
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
[ROCm/clr commit: 46a5ce4e1e ]
2017-12-04 04:48:51 -06:00
Jenkins
46a5ce4e1e
Merge 'master' into 'amd-master'
...
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
2017-12-04 04:48:51 -06:00
Jenkins
e547608c5e
Merge 'master' into 'amd-master'
...
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
[ROCm/hip commit: 45f7febc21 ]
2017-12-04 04:48:51 -06:00
Jenkins
45f7febc21
Merge 'master' into 'amd-master'
...
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
2017-12-04 04:48:51 -06:00
Ben Sander
88d6676359
Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Clean up kernel retrieval code / module management
[ROCm/clr commit: c7f9dbf789 ]
2017-12-03 18:41:27 -06:00
Ben Sander
c7f9dbf789
Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Clean up kernel retrieval code / module management
2017-12-03 18:41:27 -06:00
Ben Sander
ee0114f1f3
Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Clean up kernel retrieval code / module management
[ROCm/hip commit: d62074e3fc ]
2017-12-03 18:41:27 -06:00
Ben Sander
d62074e3fc
Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Clean up kernel retrieval code / module management
2017-12-03 18:41:27 -06:00
Ben Sander
eae70713b5
Merge pull request #276 from bensander/temp_disable_tests
...
Temporarily disable a couple tests pending some HCC work
[ROCm/clr commit: 4dfcd401b0 ]
2017-12-03 18:33:47 -06:00
Ben Sander
4dfcd401b0
Merge pull request #276 from bensander/temp_disable_tests
...
Temporarily disable a couple tests pending some HCC work
2017-12-03 18:33:47 -06:00
Ben Sander
ff543f328b
Merge pull request #276 from bensander/temp_disable_tests
...
Temporarily disable a couple tests pending some HCC work
[ROCm/hip commit: 2ae6882d4f ]
2017-12-03 18:33:47 -06:00
Ben Sander
2ae6882d4f
Merge pull request #276 from bensander/temp_disable_tests
...
Temporarily disable a couple tests pending some HCC work
2017-12-03 18:33:47 -06:00
Alex Voicu
8294d086a8
Re-sync with upstream.
...
[ROCm/clr commit: 76614f15af ]
2017-12-03 23:14:58 +00:00
Alex Voicu
76614f15af
Re-sync with upstream.
2017-12-03 23:14:58 +00:00
Alex Voicu
6e56aa7188
Re-sync with upstream.
...
[ROCm/hip commit: 5ca3176a91 ]
2017-12-03 23:14:58 +00:00
Alex Voicu
5ca3176a91
Re-sync with upstream.
2017-12-03 23:14:58 +00:00
Alex Voicu
37e40fcd40
This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
...
[ROCm/clr commit: e186bd9533 ]
2017-12-03 23:09:06 +00:00
Alex Voicu
e186bd9533
This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
2017-12-03 23:09:06 +00:00
Alex Voicu
abe3c22cf1
This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
...
[ROCm/hip commit: 5127ce67e8 ]
2017-12-03 23:09:06 +00:00
Alex Voicu
5127ce67e8
This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
2017-12-03 23:09:06 +00:00
Ben Sander
5b5bbd0b99
Merge pull request #271 from bensander/cppcheck
...
Cppcheck
[ROCm/clr commit: 6e2e029b39 ]
2017-12-02 08:36:17 -06:00
Ben Sander
6e2e029b39
Merge pull request #271 from bensander/cppcheck
...
Cppcheck
2017-12-02 08:36:17 -06:00
Ben Sander
1706feba74
Merge pull request #271 from bensander/cppcheck
...
Cppcheck
[ROCm/hip commit: 6f3ed5e3cf ]
2017-12-02 08:36:17 -06:00
Ben Sander
6f3ed5e3cf
Merge pull request #271 from bensander/cppcheck
...
Cppcheck
2017-12-02 08:36:17 -06:00
Ben Sander
345f23e6c1
Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
...
Since these are now supported directly.
[ROCm/clr commit: a431bf6ba2 ]
2017-12-02 07:44:54 -06:00
Ben Sander
a431bf6ba2
Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
...
Since these are now supported directly.
2017-12-02 07:44:54 -06:00
Ben Sander
ca1a6b3895
Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
...
Since these are now supported directly.
[ROCm/hip commit: 657e65733f ]
2017-12-02 07:44:54 -06:00
Ben Sander
657e65733f
Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
...
Since these are now supported directly.
2017-12-02 07:44:54 -06:00
Ben Sander
7d24011bdd
Update square sample for recent HIP ease-of-use improvements
...
[ROCm/hip-tests commit: 421a50e830 ]
2017-12-02 07:44:27 -06:00
Ben Sander
421a50e830
Update square sample for recent HIP ease-of-use improvements
2017-12-02 07:44:27 -06:00
Ben Sander
113335f857
Update square sample for recent HIP ease-of-use improvements
...
[ROCm/clr commit: 4192c8b54a ]
2017-12-02 07:44:27 -06:00
Ben Sander
4192c8b54a
Update square sample for recent HIP ease-of-use improvements
2017-12-02 07:44:27 -06:00
Ben Sander
2bd4446721
Update square sample for recent HIP ease-of-use improvements
...
[ROCm/hip commit: b9fa704521 ]
2017-12-02 07:44:27 -06:00
Ben Sander
b9fa704521
Update square sample for recent HIP ease-of-use improvements
2017-12-02 07:44:27 -06:00
Ben Sander
032ef0370a
Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Fix hang by purging archaisms
[ROCm/clr commit: a833ec9f7f ]
2017-12-02 07:11:55 -06:00
Ben Sander
a833ec9f7f
Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Fix hang by purging archaisms
2017-12-02 07:11:55 -06:00
Ben Sander
444c0afc2c
Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Fix hang by purging archaisms
[ROCm/hip commit: 5a642c1717 ]
2017-12-02 07:11:55 -06:00
Ben Sander
5a642c1717
Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
...
Fix hang by purging archaisms
2017-12-02 07:11:55 -06:00
foreman
369519a005
P4 to Git Change 1489603 by johtaylo@johtaylo-jtincrementor2-increment on 2017/12/02 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2548 to 2549.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2296 edit
[ROCm/clr commit: 7ad48b4fb4 ]
2017-12-02 03:13:55 -05:00
foreman
7ad48b4fb4
P4 to Git Change 1489603 by johtaylo@johtaylo-jtincrementor2-increment on 2017/12/02 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2548 to 2549.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2296 edit
2017-12-02 03:13:55 -05:00
Alex Voicu
1ba0d0ca14
Remove stray leftover comment.
...
[ROCm/clr commit: 954b7dadf7 ]
2017-12-02 00:03:10 +00:00
Alex Voicu
954b7dadf7
Remove stray leftover comment.
2017-12-02 00:03:10 +00:00
Alex Voicu
8eff1b3af4
Remove stray leftover comment.
...
[ROCm/hip commit: 02fc25de4c ]
2017-12-02 00:03:10 +00:00
Alex Voicu
02fc25de4c
Remove stray leftover comment.
2017-12-02 00:03:10 +00:00
Alex Voicu
6bdde982ff
Replace archaic use of homebrew functionality with calls to the HC maths library. This fixes a hang observed when building hipTestDeviceDouble.
...
[ROCm/clr commit: b8c80bd0b2 ]
2017-12-02 00:01:47 +00:00