-
Notifications
You must be signed in to change notification settings - Fork 745
New issue
Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.
By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.
Already on GitHub? Sign in to your account
[DevMSAN] Fix missed symbols __msan_memset & __msan_warning #16477
base: sycl
Are you sure you want to change the base?
Conversation
llvm/test/Instrumentation/MemorySanitizer/SPIRV/check_large_access_size.ll
Outdated
Show resolved
Hide resolved
libdevice/sanitizer/msan_rtl.cpp
Outdated
MSAN_MEMSET(0); | ||
MSAN_MEMSET(1); | ||
MSAN_MEMSET(3); |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
MSAN_MEMSET(0); | |
MSAN_MEMSET(1); | |
MSAN_MEMSET(3); | |
MSAN_MEMSET(0) | |
MSAN_MEMSET(1) | |
MSAN_MEMSET(3) |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
Done
const std::string Suffix = "_p" + itostr(FirstArgAS); | ||
PointerType *FirstArgPtrTy = IRB.getPtrTy(FirstArgAS); | ||
MemsetOffloadFn[FirstArgAS] = M.getOrInsertFunction( | ||
"__msan_memset" + Suffix, TLI.getAttrList(C, {1}, true), |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
"__msan_memset" + Suffix, TLI.getAttrList(C, {1}, true), | |
"__msan_memset" + Suffix, TLI.getAttrList(C, {1}, /*Signed=*/true), |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
Done
sycl::range<1>{2}, [=](sycl::id<1> ID) { | ||
B[ID] = sycl::int3{(sycl::int3)ID[0]} / B[ID]; | ||
}); |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
Is it a memset test?
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
It's hard to construct a stable memset test since the call to memset is insert by compiler.
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
LGTM
No description provided.