Microsoft MVP성태의 닷넷 이야기
VC++: 88. 하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원 [링크 복사], [링크+제목 복사],
조회: 25790
글쓴 사람
정성태 (techsharer at outlook.com)
홈페이지
첨부 파일
 

하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원

예전에 아래의 글에서 잠시 TSX 관련 이야기를 했었지요. ^^

lock-free 방식이 과연 성능에 얼마나 도움이 될까요?
; https://www.sysnet.pe.kr/2/0/1458

당연히 하스웰(Haswell)부터 되고 있겠거니 생각하는 중에... 아래의 글을 보게 되었습니다. ^^

TSX Instruction 지원 cpu는 과연 
; http://www.gamecodi.com/board/zboard.php?id=GAMECODI_Talkdev&page=1&sn1=&divpage=1&sn=off&ss=on&sc=on&select_arrange=headnum&desc=asc&no=3115

위의 덧글에 보면 엔하위키 출처의,

인텔 하스웰 마이크로아키텍처
; https://mirror.enha.kr/wiki/%EC%9D%B8%ED%85%94%20%ED%95%98%EC%8A%A4%EC%9B%B0%20%EB%A7%88%EC%9D%B4%ED%81%AC%EB%A1%9C%EC%95%84%ED%82%A4%ED%85%8D%EC%B2%98

실리콘 레벨의 버그로 인해 인텔에서 TSX disable patch 배포로 사용할수없다.

라는 내용이 있습니다. 실제로 현재 다음의 코드를,

#include "stdafx.h"
#include <immintrin.h>

int _tmain(int argc, _TCHAR* argv[])
{
    unsigned int result = _xbegin();
    if (result == _XBEGIN_STARTED)
    {
        // do transaction code 
        // ...

        _xend();
    }
    else if (result == _XABORT_DEBUG) // _XABORT_DEBUG == Transaction abort due to a debug trap 
    {
        printf("_XABORT_DEBUG\n");
    }

    return 0;
}

하스웰 아키텍쳐 지원의 CPU에서 실행하면 그냥 _XABORT_DEBUG(0x16) 값만을 반환합니다.

물론, 당연하겠지만 하스웰 지원이 안되는 컴퓨터에서 실행하는 경우에는 다음과 같이 "Illegal Instruction" 예외가 발생합니다.

The exception Illegal Instruction
An attempt was made to execute an illegal instruction.
(0xc000001d) occurred in the application at location 0x010013aa.

안타깝군요... 벤치마크 자료를 보면 꽤나 훌륭했던 것으로 보이는데...

Benchmarks : Haswell's TSX and Memory Transaction Throughput (HLE and RTM)
; http://www.sisoftware.co.uk/?d=qa&f=ben_mem_hle

어쨌든, 버그가 있으면 아무리 성능이 좋아도 소용이 없는 노릇입니다. ^^




[이 글에 대해서 여러분들과 의견을 공유하고 싶습니다. 틀리거나 미흡한 부분 또는 의문 사항이 있으시면 언제든 댓글 남겨주십시오.]







[최초 등록일: ]
[최종 수정일: 2/5/2015]

Creative Commons License
이 저작물은 크리에이티브 커먼즈 코리아 저작자표시-비영리-변경금지 2.0 대한민국 라이센스에 따라 이용하실 수 있습니다.
by SeongTae Jeong, mailto:techsharer at outlook.com

비밀번호

댓글 작성자
 



2015-02-07 07시20분
[Lyn] 아쉽게도 브로드웰에서도 고쳐지지 않았습니다.

스카이레이크 기다려야할듯
[guest]
2015-02-09 03시01분
과연, 어렵긴한가 보군요. ^^ 어쨌든, 하드웨어의 클럭 경쟁이 어려워지니 이런 유의 구현으로 확장하는 것도 재미있는 현상인 것 같습니다.
정성태
2025-07-20 02시21분
The case of the invalid instruction exception on an instruction that should never have executed
; https://devblogs.microsoft.com/oldnewthing/20250718-00/?p=111390

C++의 inline 최적화로 인해 "Illegal Instruction" 예외가 발생하는 사례를 소개합니다.
정성태

... 91  92  93  94  95  96  97  98  99  [100]  101  102  103  104  105  ...
NoWriterDateCnt.TitleFile(s)
11494정성태4/16/201816924개발 환경 구성: 362. Azure Web Apps(App Services)에 사용자 DNS를 지정하는 방법
11493정성태4/16/201818662개발 환경 구성: 361. Azure Web App(App Service)의 HTTP/2 프로토콜 지원
11492정성태4/13/201816798개발 환경 구성: 360. Azure Active Directory의 사용자 도메인 지정 방법
11491정성태4/13/201820132개발 환경 구성: 359. Azure 가상 머신에 Web Application을 배포하는 방법
11490정성태4/12/201818834.NET Framework: 739. .NET Framework 4.7.1의 새 기능 - Configuration builders [1]파일 다운로드1
11489정성태4/12/201816602오류 유형: 463. 윈도우 백업 오류 - a Volume Shadow Copy Service operation failed.
11488정성태4/12/201820951오류 유형: 462. Unhandled Exception in Managed Code Snap-in - FX:{811FD892-5EB4-4E73-A147-F1E079E36C4E}
11487정성태4/12/201818475디버깅 기술: 115. windbg - 닷넷 메모리 덤프에서 정적(static) 필드 값을 조사하는 방법
11486정성태4/11/201817547오류 유형: 461. Error MSB4064 The "ComputeOutputOnly" parameter is not supported by the "VsTsc" task
11485정성태4/11/201826237.NET Framework: 738. C# - Console 프로그램이 Ctrl+C 종료 시점을 감지하는 방법파일 다운로드1
11484정성태4/11/201827859.NET Framework: 737. C# - async를 Task 타입이 아닌 사용자 정의 타입에 적용하는 방법파일 다운로드1
11483정성태4/10/201830969개발 환경 구성: 358. "Let's Encrypt"에서 제공하는 무료 SSL 인증서를 IIS에 적용하는 방법 (2) [1]
11482정성태4/10/201822433VC++: 126. CUDA Core 수를 알아내는 방법
11481정성태4/10/201835370개발 환경 구성: 357. CUDA의 인덱싱 관련 용어 - blockIdx, threadIdx, blockDim, gridDim
11480정성태4/9/201825124.NET Framework: 736. C# - API를 사용해 Azure에 접근하는 방법 [2]파일 다운로드1
11479정성태4/9/201819508.NET Framework: 735. Azure - PowerShell로 Access control(IAM)에 새로운 계정 만드는 방법
11478정성태11/8/201922924디버깅 기술: 115. windbg - 덤프 파일로부터 PID와 환경변수 등의 정보를 구하는 방법 [1]
11477정성태4/8/201819688오류 유형: 460. windbg - sos 명령어 수행 시 c0000006 오류 발생
11476정성태4/8/201821016디버깅 기술: 114. windbg - !threads 출력 결과로부터 닷넷 관리 스레드(System.Threading.Thread) 객체를 구하는 방법
11475정성태3/28/201824093디버깅 기술: 113. windbg - Thread.Suspend 호출 시 응용 프로그램 hang 현상에 대한 덤프 분석
11474정성태3/27/201822569오류 유형: 459. xperf: error: TEST.Event: Invalid flags. (0x3ec).
11473정성태3/22/201827373.NET Framework: 734. C# - Thread.Suspend 호출 시 응용 프로그램 hang 현상파일 다운로드2
11472정성태3/22/201820522개발 환경 구성: 356. GTX 1070, GTX 960, GT 640M의 cudaGetDeviceProperties 출력 결과
11471정성태3/20/201823456VC++: 125. CUDA로 작성한 RGB2RGBA 성능 [1]파일 다운로드1
11470정성태3/20/201826698오류 유형: 458. Visual Studio - CUDA 프로젝트 빌드 시 오류 C1189, expression must have a constant value
11469정성태3/19/201819783오류 유형: 457. error MSB3103: Invalid Resx file. Could not load file or assembly 'System.Windows.Forms, ...' or one of its dependencies.
... 91  92  93  94  95  96  97  98  99  [100]  101  102  103  104  105  ...