Граф коммитов

524 Коммитов

Автор SHA1 Сообщение Дата
Ammar ELWazir 35ea06abd0 SWDEV-295522: Fixing Performance Issue
Removing DEBUG_TRACES and the unnecessary use of roctracer_op_string, made the MS app reporting 78 to 81 stable samples per second, depending on the type of the trace, while the main app without rocprof reports 100 to 106. More detailed numbers will be posted in the ticket.

Change-Id: Ida25d3bfc72047afaa27326d697be76d97564334


[ROCm/roctracer commit: e7327aaac7]
2022-04-07 00:07:24 +00:00
Ammar ELWazir f1de3ae0e5 SWDEV-307394: Fixing Download HSA-Class Issue
Exchanging the git clone of the hsa-class to a local downloaded version pushed to the roctracer repo

Change-Id: Id45a38b2d355102c2e0dee1e4bfde50398369047


[ROCm/roctracer commit: 7ee4f87b73]
2022-03-29 22:27:25 +00:00
Saravanan Solaiyappan 127ab7646d roctracer: Consider apt upgrade operation check in package scripts.
Include the upgrade operation check in the prerm script
in package.

Signed-off-by: Saravanan Solaiyappan <saravanan.solaiyappan@amd.com>
Change-Id: I1504ce96a27d21d9c3d9bafc0dea8055398adc99


[ROCm/roctracer commit: bfea525ff3]
2022-03-21 23:43:19 -04:00
Saurabh Verma 553d8a0da3 Merge "SWDEV-295871: [MSRCHA-130] Unable to filter API using .txt or .xml -Part-2 of MSRCHA-128. Made xml input more robust to accept both spaces and commas in xml array." into amd-staging
[ROCm/roctracer commit: 43657de4d2]
2022-03-18 10:13:31 -04:00
Ammar ELWazir 1029cc418e SWDEV-328300: supporting centos-9 for roctracer
Changing pthread_yield() to sched_yield() as pthread_yield() is deprecated in CentOS 9

Change-Id: I2961b61374e36995d0835f0e65b26c35f5eb8715


[ROCm/roctracer commit: 43a36f8dd5]
2022-03-18 01:26:39 +00:00
Saurabh Verma e1f9f82198 SWDEV-295871: [MSRCHA-130] Unable to filter API using .txt or .xml -Part-2 of MSRCHA-128. Made xml input more robust to accept both spaces and commas in xml array.
Change-Id: I3900fdf91cd0b893fadd9dfc958030effc5663db


[ROCm/roctracer commit: 37ed31087a]
2022-03-17 17:16:17 -05:00
Saurabh Verma daa23130ad SWDEV-295871 : [MSRCHA-130] Unable to filter API using .txt or .xml - Part-2 of MSRCHA-128. Fixed constructor ordering issue of global variables hip_api_vec and hsa_api_vec by wrapping themin static getter functions
Change-Id: I2dae5e196118fcab696b2365b24281f05d9d0f88


[ROCm/roctracer commit: aee8102fa6]
2022-03-14 16:07:58 -04:00
Ammar ELWazir 5daf0bcd13 SWDEV-296010: Fixing RPATH & CMAKE files
Removing the RPATH skip & Removing the install path that was defined CMakelist

Change-Id: Icf374b9548fc7b24e99a1b5ab9720ce6d775abf8


[ROCm/roctracer commit: 8098ec6acf]
2022-03-09 19:16:08 -06:00
Ranjith Ramakrishnan 472330b728 File reorganization with backward compatibility
Package installed /opt/rocm
Soft links and wrapper header files installed /opt/rocm/roctracer for backward compatibility
tracer_tool library renamed to roctracer_tool and installed in /opt/rocm/lib/roctracer

Change-Id: Ica7518c5ef2e591715121cbc942b69dff29233d3


[ROCm/roctracer commit: bc19ae71eb]
2022-03-04 04:03:51 -08:00
Ranjith Ramakrishnan 9b1793bd39 Merge "SWDEV-291455: Prefer rocm include path to hip include path" into amd-staging
[ROCm/roctracer commit: c037ccb95e]
2022-02-15 14:43:32 -05:00
Ranjith Ramakrishnan a3c738ff30 SWDEV-291455: Prefer rocm include path to hip include path
Change-Id: I1fa96e72169fac689a3a2ed38e988d7f5d18bf04


[ROCm/roctracer commit: ebda880c4a]
2022-02-14 14:21:32 -08:00
Kiumars Sabeti 55299c1d75 SWDEV-322312 [ASAN] [roctracer] RPM packages are generated while building roctracer for UBUNTU
To fix the issue we modified CMakeLists.txt as described in Sparry Icarus comment

Change-Id: Ie9ca16cfcfb7b7a9a858f0fb1f5071923c787313


[ROCm/roctracer commit: 554011e767]
2022-02-11 19:21:17 +00:00
Kiumars Sabeti fa57056629 SWDEV-322312: RPM packages are generated while build roctracer for UBUNTU
replaced -DCPACK_GENERATOR=DEB

Change-Id: I9f6d4d652e7cad510343731948675f0cd4398ef4


[ROCm/roctracer commit: cec4cb2538]
2022-02-11 08:33:17 +00:00
kiumars f7c3908e62 replace the set of CMAKE_SHARED_LINKER_FLAGS with add_link_options.
Change-Id: I2696ccd53b234e700e1464b0b3852aac1e3fc3b3


[ROCm/roctracer commit: e56146ff7c]
2022-02-03 12:55:15 -05:00
Ammar ELWazir 4cca362f20 SWDEV-318551: Adding License file for tracer
Making the new License file, Adding support in the CMakeLists.txt

Change-Id: I43862b8b7f3025ae6200aeb442ea70c7993a7349


[ROCm/roctracer commit: b721e3209e]
2022-01-26 13:39:31 -05:00
Icarus Sparry 7e622b9075 Forcibly disable parallelism
The manually written Makefiles in the test directory are not safe to
use by more than one job. For example we see things like
	all: clean $(EXECUTABLE)
which says that the 'all' target depends on the 'clean' and
'$(EXECUTABLE)' targets. If make is invoked with -j2 then the clean
and '${EXECUTABLE}' can be built in parallel, so the clean can delete
things whilst they are being built!

Change-Id: I9c56db4c629081b8d812dad45dfd4afde10e481f
Signed-off-by: Icarus Sparry <icarus.sparry@amd.com>


[ROCm/roctracer commit: 8ea268b3f4]
2021-10-31 15:19:36 -07:00
Ammar ELWazir 023cb806f9 SWDEV-275232: Replaced the use of on_exit()
on_exit() registered exit_handler function, but in the case of OpenMP applications the registered exit func exit_handler was called after the dlclose of the library. So we removed exit_handler from roctracer as it is already handled in both rocprofiler and rocprof script.

Change-Id: I7c3d42e6ccc282e713b48b4a7faec4935e7a2600


[ROCm/roctracer commit: aa41554130]
2021-10-09 17:36:36 -04:00
Ammar ELWazir 606d3dd8e8 SWDEV-298155: Fixing HSA-CLASS REV
Adding the latest commit to pull from the hsa-class git repo that includes the fix for SWDEV-298155
"Fixing the typo in evt_stats.h" https://github.com/ROCmSoftwarePlatform/hsa-class/commit/e6456a6d93cc6d8bcc59bd6ea24f27146f86ff4c

Change-Id: I9984de8ec9204a6cf47a25ce4ac42852473c56c9


[ROCm/roctracer commit: 99e2f37c81]
2021-09-29 12:27:15 -04:00
Saurabh Verma 3b16547bf6 SWDEV-295878 Fix for seg fault when using --trace-start off
Change-Id: Ic76d814b3591f72db18319d78f34596dae1ddfee


[ROCm/roctracer commit: a7cd80b716]
2021-08-31 16:46:59 -05:00
Ammar Elwazir a40f9816e5 Merge "SWDEV-294319 & SWDEV-294321 Added support for missing functions" into amd-staging
[ROCm/roctracer commit: 02d27d06e5]
2021-08-12 03:15:40 -04:00
Ammar ELWazir fe9f4c9d87 SWDEV-294248 (Fixing Race Conditions):
Fixing race conditions that happened when enabling trace-period feature on the following code:
#include <hip/hip_runtime.h>
__global__ void
kernel ()
{
}
int
main (int argc, char **argv)
{
  for (size_t i = 0; i < 10000; ++i) {
    hipLaunchKernelGGL (kernel, 1, 1, 0, 0);
    hipDeviceSynchronize ();
  }
  return 0;
}

Change-Id: I4eb88a4a71efbad0f6483e7fb6e8e0c6a662860b


[ROCm/roctracer commit: 513460bd41]
2021-08-11 22:48:55 -04:00
Ammar Elwazir 8b48f6ad7e Merge "Fixing correlation_id_map" into amd-staging
[ROCm/roctracer commit: 53fa06ad66]
2021-08-11 21:44:59 -04:00
Ammar Elwazir e52fc25af9 Merge "Cosmetic change" into amd-staging
[ROCm/roctracer commit: 682ebba1c2]
2021-08-11 20:47:53 -04:00
Ammar ELWazir bf410d1747 SWDEV-294319 & SWDEV-294321 Added support for missing functions
Added Support for launch kernel functions to fill_api_db

Change-Id: Ie8749806214d6e283c3d408d8019f178f42018bf


[ROCm/roctracer commit: 8396836c25]
2021-08-11 11:42:21 -04:00
Ammar ELWazir 77ef6e38dc Cosmetic change
Fixing variable names and removing un-needed references

Change-Id: I3ed2cee89e7dc599caf1726fe1eab1a913e5a93d


[ROCm/roctracer commit: b02586c587]
2021-08-09 14:13:57 -04:00
Ammar ELWazir fec4a850bb Fixing correlation_id_map
Changing correlation_id_map to static instance instead of being a pointer and fixing the corresponding references

Change-Id: Id8a481a90b46831f91985a7e0523fd2869991aeb


[ROCm/roctracer commit: 1e3ed06a9a]
2021-08-09 14:05:52 -04:00
Christophe Paquot a9f6522a41 SWDEV-295205 - Remove KFD domain from roctracer
Change-Id: I2771cf43aa115bb466531bf887f7cc75e187f2ef


[ROCm/roctracer commit: e5e1258ef8]
2021-07-22 10:12:45 -07:00
Christophe Paquot ae9c760305 SWDEV-281658 - Preserve the callback IDs enum ordering
Use HIP_API_ID_NONE to detect unsupported API instead of
HIP_API_ID_NUMBER which can grow with a new version of the API.
This HIP_API_ID_NONE enum has a fixed value of 0 so the
HIP_API_IDs really start at FIRST.

Change-Id: I760aa50ddf6fa6d46bf20555ad7d429335a53f97


[ROCm/roctracer commit: b04dfd5fdf]
2021-06-30 09:52:20 -04:00
Freddy Paul 1c6c8def17 roctracer:All libraries need to be installed with LIBRARY TAG
Cmake will do the post processing required for RPATH or any other
needed for the libraries only if installed as libraries not as
regular files

FIX: SWDEV-287893
Change-Id: I9cf478fcd23b9f2e8b3bdd81aa566cad3ec2a5e3


[ROCm/roctracer commit: 1cc934204f]
2021-05-26 12:15:25 -04:00
Rachida Kebichi 99ae6ad86a SWDEV-284863 Fixed several issues preventing memcpy info dump in csv
Change-Id: I4c6323311ce8314296e81a9b9b5d8adb485e0aa8


[ROCm/roctracer commit: e5dd1e9b85]
2021-05-25 11:10:52 -04:00
Laurent Morichetti 77c83db3ef Fix random bugs discovered while reading the code
In HsaTimer::correlated_pair_ns, the time ID should be used to
select the clock ID passed to clock_gettime.

In MemoryPool::allocator_default, pass the correct value to realloc.

Change-Id: I5d10c0994c07fdeadd99c81deba4e71a4f579523


[ROCm/roctracer commit: 297b613604]
2021-05-20 21:22:16 -04:00
Laurent Morichetti 61e044e67c Make HIP_VDI the default
As this snippet shows, HCC is no longer supported by roctracer:

#if HIP_VDI
...
#else
#error HCC support dropped
#endif

Removed HIP_VDI from the CMakeLists.txt, and the source code.

Change-Id: Ib273da2a5af6d67fa1b021a7eca3ff785c8b9c73


[ROCm/roctracer commit: 8fb3cdb30b]
2021-05-20 21:20:27 -04:00
Rachida Kebichi 4214723eda SWDEV-283958 Workaround for unnamed structs
CppHeaderParser has limited support for unnamed structs. It leaves the
name empty so this results in classes (a.k.a structs) having trailing '::'
characters, also giving no way to distingush two unnamed structs at the
same level of nesting. An example are the inner structs of
hipExternalSemaphoreSignalParams. The workaround consists in skipping
over these, so they are not generated in the output header file
which lists all ostream ops<<. Only the inner unnamed structs are skipped,
the rest is processed as it should.

Change-Id: I17439c46095469b7adb7aee0b0f0b3d234aabc11


[ROCm/roctracer commit: faada3e569]
2021-05-07 15:57:30 -04:00
Freddy Paul 819a91bf15 roctracer:update with case-sensitivity email
All packages should have a valid email for contact.

SWDEV-257322

Change-Id: I3a489bde4283545cba2ee377edc5a8b7adb75116


[ROCm/roctracer commit: 7bcac00f35]
2021-05-03 11:47:42 -07:00
Freddy Paul b91aff7fa1 roctracer:Add maintainer email in package.
All packages should have a valid email for contact.

SWDEV-257322

Change-Id: I04b7d5ccc618b0a0907a75a92f50c9da64c3ff32


[ROCm/roctracer commit: 0cff9b7dc9]
2021-04-30 11:35:59 -07:00
Kent Russell e37c63ea09 roctracer: Support static thunk
Add numa lib as this will be required with a static thunk
Look for static thunk of shared thunk cannot be found

Signed-off-by: Kent Russell <kent.russell@amd.com>
Change-Id: I5de63e0a56a8946132ccbb7140a19a82a70b951d


[ROCm/roctracer commit: 5c9329aec8]
2021-04-27 12:56:56 -04:00
Laurent Morichetti aa5937fbe1 Fix a compilation error with gcc-9.3.0
On Ubuntu 20.04, in Release mode, gcc fails with this error:

In file included from /usr/include/string.h:495,
                 from /opt/rocm/include/hsa/hsa_api_trace.h:57,
                 from ../roctracer/src/util/hsa_rsrc_factory.h:29,
                 from ../roctracer/src/util/hsa_rsrc_factory.cpp:25:
In function ‘char* strncpy(char*, const char*, size_t)’,
    inlined from ‘const util::AgentInfo* util::HsaRsrcFactory::AddAgentInfo(hsa_agent_t)’ at ../roctracer/src/util/hsa_rsrc_factory.cpp:323:12:
/usr/include/x86_64-linux-gnu/bits/string_fortified.h:106:34: error: ‘char* __builtin___strncpy_chk(char*, const char*, long unsigned int, long unsigned int)’ specified bound depends on the length of the source argument [-Werror=stringop-overflow=]
  106 |   return __builtin___strncpy_chk (__dest, __src, __len, __bos (__dest));
      |          ~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
../roctracer/src/util/hsa_rsrc_factory.cpp: In member function ‘const util::AgentInfo* util::HsaRsrcFactory::AddAgentInfo(hsa_agent_t)’:
../roctracer/src/util/hsa_rsrc_factory.cpp:322:39: note: length computed here
  322 |     const int gfxip_label_len = strlen(agent_info->name) - 2;
      |                                 ~~~~~~^~~~~~~~~~~~~~~~~~

The error is caused by the following 2 lines:

    const int gfxip_label_len = strlen(agent_info->name) - 2;
    strncpy(agent_info->gfxip, agent_info->name, gfxip_label_len);

The size argument to strncpy should not depend on the input string.

Since the terminating character is not considered (the copy is at
most len - 2 bytes), using memcpy is preferable. Also, make sure
the destination does not overflow by clamping the size.

Change-Id: I37c5c45418e7c31a017581b6c16e5d47cd61aec5


[ROCm/roctracer commit: 38009bfba4]
2021-04-19 22:57:51 -07:00
Rachida Kebichi a5571976e5 SWDEV-281008 replace hcc_detail by amd_detail
Change-Id: I180b18f9e1fae40c923d6210901f06cba14e8f13


[ROCm/roctracer commit: 6267df36e4]
2021-04-14 11:18:38 -04:00
Rachida Kebichi ff4cabdf4e SWDEV-272488 append to CMAKE_CXX_FLAGS instead of override
Change-Id: Ib5e6856944bf54b2161cba9ac24adda57fdf8a9a


[ROCm/roctracer commit: 8c3bd6817e]
2021-04-06 15:45:44 -04:00
Evgeny Shcherbakov 95f15bf72c Merge "fxing gfxip label" into amd-staging
[ROCm/roctracer commit: 26fd08feae]
2021-04-03 01:31:34 -04:00
Rachida Kebichi d78eaf664f SWDEV-255637 support for hsa_amd_memory_async_copy_rect
Change-Id: I5db6484c30427712c56b59862e748118a3f079c2


[ROCm/roctracer commit: 06271806d4]
2021-03-31 10:02:06 -04:00
Cole Nelson 4171d2be0d Merge "CMakeLists.txt: add ENABLE_LDCONFIG to support multi-version install" into amd-staging
[ROCm/roctracer commit: 3018150e53]
2021-03-30 15:37:50 -04:00
Rachida Kebichi 28faba40a7 SWDEV-271503 Fixed core dump
Change-Id: Ia582a27482581c3b81c42da0add9f6743898da6c


[ROCm/roctracer commit: ad5b463912]
2021-03-30 14:06:56 -04:00
Evgeny 1eeb601150 fxing gfxip label
Change-Id: Ic22d828b38da8afc5a232c2f2eb5de5410844b70


[ROCm/roctracer commit: 2287da5e28]
2021-03-28 08:11:58 +00:00
Cole Nelson df5618cd66 CMakeLists.txt: add ENABLE_LDCONFIG to support multi-version install
Depends-On: I58fdf1d0b4e864b5a61ffe8e335d430d424811ab
Change-Id: I1eeb778ac58a2c4b588244adc3112ecb1aa15217
Signed-off-by: Cole Nelson <cole.nelson@amd.com>


[ROCm/roctracer commit: 16d4a79562]
2021-03-27 15:36:02 -07:00
Evgeny 76f7c9a5fd SWDEV-267198 : adding gpu index to hsa_handles file
Change-Id: I6ddba45ab31fff97a1f85f889c56693accf8f5bc


[ROCm/roctracer commit: 1c77416a6c]
2021-03-09 15:37:44 -06:00
Evgeny fc65a545a7 SWDEV-251491 : fixing tracing on exit
Change-Id: I1bf2a6093331e7a08179b9f64394c5c49206ef0e


[ROCm/roctracer commit: 912cfd4cf8]
2020-12-25 01:49:44 -05:00
Evgeny b81697c07e SWDEV-251491 : disabling tracing on exit
Change-Id: Ifd5f0fbad70afa1e79da8b4b9aa639d899cbea76


[ROCm/roctracer commit: 99eee45546]
2020-12-22 04:55:07 -05:00
Rachida Kebichi bbf605467b SWDEV-259683 HIP API records filtering
Change-Id: I43ca5e022d2c055b6a9bc2c09b4276b490a4b986


[ROCm/roctracer commit: 2d31848c44]
2020-12-16 16:29:36 -05:00
Evgeny Shcherbakov 608a087451 Merge "calling python3 explictely" into amd-staging
[ROCm/roctracer commit: 3e4539c95d]
2020-12-16 16:01:57 -05:00