@@ -53,7 +53,7 @@ struct AMDGPUImplicitArgsTyCOV4 {
5353 uint8_t Unused[56 ];
5454};
5555
56- uint32_t getImplicitArgsSize (uint16_t Version) {
56+ inline uint32_t getImplicitArgsSize (uint16_t Version) {
5757 return Version < ELF::ELFABIVERSION_AMDGPU_HSA_V5
5858 ? sizeof (AMDGPUImplicitArgsTyCOV4)
5959 : sizeof (AMDGPUImplicitArgsTy);
@@ -173,44 +173,44 @@ class KernelInfoReader {
173173 if (!V.first .isString ())
174174 return Error::success ();
175175
176- const auto isKey = [](const msgpack::DocNode &DK, StringRef SK) {
176+ const auto IsKey = [](const msgpack::DocNode &DK, StringRef SK) {
177177 return DK.getString () == SK;
178178 };
179179
180- const auto getSequenceOfThreeInts = [](msgpack::DocNode &DN,
180+ const auto GetSequenceOfThreeInts = [](msgpack::DocNode &DN,
181181 uint32_t *Vals) {
182182 assert (DN.isArray () && " MsgPack DocNode is an array node" );
183183 auto DNA = DN.getArray ();
184184 assert (DNA.size () == 3 && " ArrayNode has at most three elements" );
185185
186- int i = 0 ;
186+ int I = 0 ;
187187 for (auto DNABegin = DNA.begin (), DNAEnd = DNA.end (); DNABegin != DNAEnd;
188188 ++DNABegin) {
189- Vals[i ++] = DNABegin->getUInt ();
189+ Vals[I ++] = DNABegin->getUInt ();
190190 }
191191 };
192192
193- if (isKey (V.first , " .name" )) {
193+ if (IsKey (V.first , " .name" )) {
194194 KernelName = V.second .toString ();
195- } else if (isKey (V.first , " .sgpr_count" )) {
195+ } else if (IsKey (V.first , " .sgpr_count" )) {
196196 KernelData.SGPRCount = V.second .getUInt ();
197- } else if (isKey (V.first , " .sgpr_spill_count" )) {
197+ } else if (IsKey (V.first , " .sgpr_spill_count" )) {
198198 KernelData.SGPRSpillCount = V.second .getUInt ();
199- } else if (isKey (V.first , " .vgpr_count" )) {
199+ } else if (IsKey (V.first , " .vgpr_count" )) {
200200 KernelData.VGPRCount = V.second .getUInt ();
201- } else if (isKey (V.first , " .vgpr_spill_count" )) {
201+ } else if (IsKey (V.first , " .vgpr_spill_count" )) {
202202 KernelData.VGPRSpillCount = V.second .getUInt ();
203- } else if (isKey (V.first , " .private_segment_fixed_size" )) {
203+ } else if (IsKey (V.first , " .private_segment_fixed_size" )) {
204204 KernelData.PrivateSegmentSize = V.second .getUInt ();
205- } else if (isKey (V.first , " .group_segement_fixed_size" )) {
205+ } else if (IsKey (V.first , " .group_segement_fixed_size" )) {
206206 KernelData.GroupSegmentList = V.second .getUInt ();
207- } else if (isKey (V.first , " .reqd_workgroup_size" )) {
208- getSequenceOfThreeInts (V.second , KernelData.RequestedWorkgroupSize );
209- } else if (isKey (V.first , " .workgroup_size_hint" )) {
210- getSequenceOfThreeInts (V.second , KernelData.WorkgroupSizeHint );
211- } else if (isKey (V.first , " .wavefront_size" )) {
207+ } else if (IsKey (V.first , " .reqd_workgroup_size" )) {
208+ GetSequenceOfThreeInts (V.second , KernelData.RequestedWorkgroupSize );
209+ } else if (IsKey (V.first , " .workgroup_size_hint" )) {
210+ GetSequenceOfThreeInts (V.second , KernelData.WorkgroupSizeHint );
211+ } else if (IsKey (V.first , " .wavefront_size" )) {
212212 KernelData.WavefronSize = V.second .getUInt ();
213- } else if (isKey (V.first , " .max_flat_workgroup_size" )) {
213+ } else if (IsKey (V.first , " .max_flat_workgroup_size" )) {
214214 KernelData.MaxFlatWorkgroupSize = V.second .getUInt ();
215215 }
216216
@@ -273,9 +273,10 @@ class KernelInfoReader {
273273
274274// / Reads the AMDGPU specific metadata from the ELF file and propagates the
275275// / KernelInfoMap
276- Error readAMDGPUMetaDataFromImage (MemoryBufferRef MemBuffer,
277- StringMap<KernelMetaDataTy> &KernelInfoMap,
278- uint16_t &ELFABIVersion) {
276+ inline Error
277+ readAMDGPUMetaDataFromImage (MemoryBufferRef MemBuffer,
278+ StringMap<KernelMetaDataTy> &KernelInfoMap,
279+ uint16_t &ELFABIVersion) {
279280 Error Err = Error::success (); // Used later as out-parameter
280281
281282 auto ELFOrError = object::ELF64LEFile::create (MemBuffer.getBuffer ());
0 commit comments