Lines Matching defs:Agent

140 Error iterateAgentISAs(hsa_agent_t Agent, CallbackTy Cb) {
141   hsa_status_t Status = iterate<hsa_isa_t>(hsa_agent_iterate_isas, Agent, Cb);
147 Error iterateAgentMemoryPools(hsa_agent_t Agent, CallbackTy Cb) {
149       hsa_amd_agent_iterate_memory_pools, Agent, Cb);
193 Error getTargetTripleAndFeatures(hsa_agent_t Agent,
195   auto Err = hsa_utils::iterateAgentISAs(Agent, [&](hsa_isa_t ISA) {
316   /// Returns if the \p Agent can access the memory pool.
317   bool canAccess(hsa_agent_t Agent) {
320             Agent, MemoryPool, HSA_AMD_AGENT_MEMORY_POOL_INFO_ACCESS, &Access))
329     for (hsa_agent_t Agent : Agents) {
332               getAttr(Agent, HSA_AMD_AGENT_MEMORY_POOL_INFO_ACCESS, Access))
363   Error getAttr(hsa_agent_t Agent, hsa_amd_agent_memory_pool_info_t Kind,
367         hsa_amd_agent_memory_pool_get_info(Agent, MemoryPool, Kind, &Value);
686   Error init(GenericDeviceTy &Device, hsa_agent_t Agent, int32_t QueueSize) {
690         hsa_queue_create(Agent, QueueSize, HSA_QUEUE_TYPE_MULTI, callbackError,
1025   hsa_agent_t Agent;
1302       return hsa_utils::asyncMemCopy(UseMultipleSdmaEngines, Dst, Agent, Src,
1303                                      Agent, CopySize, 1, &InputSignalRaw,
1307     return hsa_utils::asyncMemCopy(UseMultipleSdmaEngines, Dst, Agent, Src,
1308                                    Agent, CopySize, 0, nullptr,
1344               UseMultipleSdmaEngines, Inter, Agent, Src, Agent, CopySize, 1,
1349                                              Agent, Src, Agent, CopySize, 0,
1441       return hsa_utils::asyncMemCopy(UseMultipleSdmaEngines, Dst, Agent, Inter,
1442                                      Agent, CopySize, 1, &InputSignalRaw,
1445     return hsa_utils::asyncMemCopy(UseMultipleSdmaEngines, Dst, Agent, Inter,
1446                                    Agent, CopySize, 0, nullptr,
1634         NextQueue(0), Agent(HSAAgent) {}
1641     if (auto Err = Queues.front().init(Device, Agent, QueueSize))
1698     if (auto Err = Queues[Index].init(Device, Agent, QueueSize))
1719   hsa_agent_t Agent;
1839     for (hsa_agent_t Agent : Agents) {
1841           Agent, [&](hsa_amd_memory_pool_t HSAMemoryPool) {
1898                  AMDHostDeviceTy &HostDevice, hsa_agent_t Agent)
1910         OMPX_ApuMaps("OMPX_APU_MAPS", false), AMDGPUStreamManager(*this, Agent),
1911         AMDGPUEventManager(*this), AMDGPUSignalManager(*this), Agent(Agent),
2005     if (auto Err = hsa_utils::getTargetTripleAndFeatures(Agent, Targets))
2043     Agent = {0};
2354                                              Agent, PinnedPtr, Agent, Size, 0,
2414                                              PinnedPtr, Agent, TgtPtr, Agent,
2489       DeviceInfo->Device = reinterpret_cast<void *>(Agent.handle);
2787         hsa_agent_get_info(Agent, (hsa_agent_info_t)Kind, &Value);
2793     return hsa_agent_get_info(Agent, (hsa_agent_info_t)Kind, &Value);
2797   hsa_agent_t getAgent() const override { return Agent; }
2806         Agent, [&](hsa_amd_memory_pool_t HSAMemoryPool) {
2931   hsa_agent_t Agent;
3010   hsa_agent_t Agent = AMDGPUDevice.getAgent();
3014       Executable, SymbolName.data(), &Agent, &Symbol);
3036     : Agent(Device.getAgent()), Queue(nullptr),
3127     auto Err = hsa_utils::iterateAgents([&](hsa_agent_t Agent) {
3131           hsa_agent_get_info(Agent, HSA_AGENT_INFO_DEVICE, &DeviceType);
3139         Status = hsa_agent_get_info(Agent, HSA_AGENT_INFO_FEATURE, &Features);
3141           KernelAgents.push_back(Agent);
3143         HostAgents.push_back(Agent);
3495       [&](hsa_agent_t Agent) { return MemoryPool->canAccess(Agent); });
3543                   std::back_inserter(Agents), [&](hsa_agent_t Agent) {
3544                     return MemoryPool->canAccess(Agent);