Register Guidelines E-Books Search Today's Posts Mark Forums Read

Go Back   MobileRead Forums > E-Book Readers > Amazon Kindle > Kindle Developer's Corner

Notices

Reply
 
Thread Tools Search this Thread
Old 10-19-2012, 01:56 PM   #721
knc1
Embedded Cheerleader
knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.knc1 ought to be getting tired of karma fortunes by now.
 
knc1's Avatar
 
Posts: 6,665
Karma: 5850002
Join Date: Feb 2012
Device: Too many.
Or that is stored in a locked section of the flash, and the code did not unlock it first.
knc1 is offline   Reply With Quote
Old 10-19-2012, 02:41 PM   #722
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by adi23 View Post
Maybe have you missed something?
It could be so. But there are no more appropriate defines in bist U-Boot config to copy (as for me).

BTW, with U-Boot size about 80kb you're overwriting MMU table (which is located right after OCRAM). But it looks like in this case it's not dangerous at all.
eureka is offline   Reply With Quote
Old 10-19-2012, 03:59 PM   #723
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by adi23 View Post
Also, i could modify the custom u-boot again in order to load some data in memory, but i don't know exactly how should i do this, or what data should i load.
As you can access U-Boot through serial, you can try loadb command:
  • build bist U-boot (i.e. without TYPE=prod), but I think you should make clean beforehand if you've built ordinary U-Boot in the same directory previously
  • comment all mmc-related calls in function do_bist at file common/cmd_boot.c
  • add #define CONFIG_CMD_LOADB to include/configs/imx50_yoshi.h
  • build ordinary U-Boot (i.e. with TYPE=prod), but again don't forget make clean beforehand
  • load ordinary U-Boot and in serial console load bist U-Boot into memory with command loadb 0x79800000 (0x79800000 is the value of CONFIG_BISTADDR define)
  • issue command bist to run bist U-Boot loaded into memory (or bist fastboot to load straight into fastboot mode)
Again, I didn't try it, I've just read sources and googled a bit.

Last edited by eureka; 10-19-2012 at 05:09 PM. Reason: add link to howto about loadb command
eureka is offline   Reply With Quote
Old 10-19-2012, 04:13 PM   #724
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by eureka View Post
BTW, with U-Boot size about 80kb you're overwriting MMU table (which is located right after OCRAM). But it looks like in this case it's not dangerous at all.
Ha, imx_usb_loader spits out errors if u-boot.bin size goes beyond free OCRAM area. Also, 4kb of u-boot.bin takes not the U-Boot itself, but flash header or something.

Log of errors is here:
Spoiler:
Code:
parse mx50_usb_work.conf
15a2:0052(KindleTouch) bConfigurationValue =1
Interface 0 claimed
report 1, wrote 16 bytes, err=0
report 3, read 5 bytes, err=0
read=56 78 78 56
fastboot.bin
No dcd table, barker=402000d1
dcd_ptr=0x00000000

loading binary file(fastboot.bin) to f8006000, skip=0, fsize=800 type=aa

<<<2048, 2048 bytes>>>
jumping to 0xf8006400
j3 in err=0, last_trans=5  56 78 78 56
j4 in err=-7, last_trans=0  00 00 00 00
report 1, wrote 16 bytes, err=0
report 3, read 5 bytes, err=0
read=56 78 78 56
jump_mode 2 plug=1 err=0
fastboot.bin
header_max=1000

loading binary file(fastboot.bin) to f8007000, skip=0, fsize=1290c type=aa
out err=-9, last_trans=0 c=0x190c max=0x400 transferSize=0x11000 retry=0
out err=-9, last_trans=0 c=0x190c max=0x200 transferSize=0x11000 retry=1
out err=-9, last_trans=0 c=0x190c max=0x100 transferSize=0x11000 retry=2
out err=-9, last_trans=0 c=0x190c max=0x80 transferSize=0x11000 retry=3
out err=-9, last_trans=0 c=0x190c max=0x40 transferSize=0x11000 retry=4
out err=-9, last_trans=0 c=0x190c max=0x20 transferSize=0x11000 retry=5
out err=-9, last_trans=0 c=0x190c max=0x10 transferSize=0x11000 retry=6
out err=-9, last_trans=0 c=0x190c max=0x8 transferSize=0x11000 retry=7
out err=-9, last_trans=0 c=0x190c max=0x10 transferSize=0x11000 retry=8
out err=-9, last_trans=0 c=0x190c max=0x8 transferSize=0x11000 retry=9
out err=-9, last_trans=0 c=0x190c max=0x10 transferSize=0x11000 retry=10

<<<76044, 69632 bytes>>>
3 in err=-7, last_trans=0  00 00 00 00
4 in err=-7, last_trans=0  00 00 00 00
jumping to 0xf800742c
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
jump_command err=-9, last_trans=0
Did you see that summary line: <<<76044, 69632 bytes>>> (i.e loaded 69632 of 76044 bytes)? 69632 bytes is 68kb. 68kb = 72kb of free OCRAM area - 4kb of flash header in u-boot.bin.

It's just an observation, nothing more.
eureka is offline   Reply With Quote
Old 10-19-2012, 04:16 PM   #725
ixtab
(offline)
ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.
 
ixtab's Avatar
 
Posts: 2,903
Karma: 6677557
Join Date: Dec 2011
Device: K3, K4, K5, KPW, KPW2
K5 u-boot bist

FWIW, here's a compiled u-boot bist. It was compiled straight from the Amazon-published sources for the Kindle Touch (i.e., no bells and whistles, no custom modifications).
Attached Files
File Type: zip k5_uboot_bist.zip (63.4 KB, 205 views)
ixtab is offline   Reply With Quote
Old 10-19-2012, 04:22 PM   #726
ixtab
(offline)
ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.
 
ixtab's Avatar
 
Posts: 2,903
Karma: 6677557
Join Date: Dec 2011
Device: K3, K4, K5, KPW, KPW2
Quote:
Originally Posted by eureka View Post
Ha, imx_usb_loader spits out errors if u-boot.bin size goes beyond free OCRAM area. Also, 4kb of u-boot.bin takes not the U-Boot itself, but flash header or something.
I guess you meant to say: everything before offset 0x400 (that's 1 kB, not 4 ). This is documented somewhere deep inside the manual... found it: it's section 6.6 (page 458).
ixtab is offline   Reply With Quote
Old 10-19-2012, 04:47 PM   #727
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by ixtab View Post
I guess you meant to say: everything before offset 0x400 (that's 1 kB, not 4 ). This is documented somewhere deep inside the manual... found it: it's section 6.6 (page 458).
I was saying about log's content. Just look at it: there is successful loading of "file" with size 0x800 at address 0xf8006000 and then failed load of "file" with size 0x1290c at address 0xf8007000.

(There were no first or second file, it was the same file, just with two IVT)

Hmmm, OK, I was wrong, flash header takes 2 kb (0x800=2048). But anyway, second "file" (i.e. U-Boot itself) is loaded with offset of 0x1000 (4096) from start of free OCRAM area.

OK, 2kb is perfectly matching with that table 6-22 from Reference Manual: "eMMC" - "Initial image size: 2Kbyte"

All of it certainly isn't a big discovery, as flash_header.S is freely available for researching in board directory in U-Boot sources. I've just lost control because of failed downloading of "big" U-Boot into OCRAM (does MfgTools really allow it?) and posted junk
eureka is offline   Reply With Quote
Old 10-20-2012, 04:55 AM   #728
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
U-Boot (for Kindle Touch) that includes fastboot "server", automatically goes straight into fastboot mode on booting and could be loaded with imx_usb_loader. Use Yifan Lu's fastboot client for sending fastboot commands.

This U-Boot is intentionally and rudely crippled in an effort to make room for fastboot code. Only following fastboot commands are expected to work: getvar, setvar, download, flash and reboot. Other fastboot commands may not work or return completely wrong result without any warnings or fail in funky way. Serial access to U-Boot console should not work at all.

Beginning of old (original) content:
Spoiler:
With the help of hammer, chisel and pile of damns I've managed to make ordinary U-Boot that includes fastboot "server", automatically goes straight into fastboot mode on booting and could be loaded with imx_usb_loader. I've used Yifan Lu's fastboot client to get idme var and it worked. But I have no desire to overwrite my partitions now (to test flash command) Note, that check command will not return real result (as crc32 checking function was removed to decrease file size).

Of course, I can't say for sure, whether it really does not require bist U-Boot, as I has no serial console access and can't check the log. So sorry for disappointment if it will not work as described. Report me and I will delete attachment.
(Patch to original U-Boot source will be provided soon, if it really will work; just let me day or two to tidy up that mess of impulsive edits UPD: done.)
Attached Files
File Type: bin fastboot.bin (71.7 KB, 68 views)

Last edited by eureka; 12-22-2013 at 12:51 PM. Reason: replace fastboot.bin with new, current version
eureka is offline   Reply With Quote
Old 10-20-2012, 09:07 AM   #729
geekmaster
Всё гениальное просто.
geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.
 
geekmaster's Avatar
 
Posts: 5,070
Karma: 6789001
Join Date: Nov 2011
Location: Щедрость не имеет пределов.
Device: *.*
Quote:
Originally Posted by eureka View Post
With the help of hammer, chisel and pile of damns I've managed to make oridinary U-Boot that includes fastboot "server", automatically goes straight into fastboot mode on booting and could be loaded with imx_usb_loader. I've used Yifan Lu's fastboot client to get idme var and it worked. And I have no desire to overwrite my partitions now Note, that check command will not return real result (as crc32 checking function was removed to decrease file size).

Of course, I can't say for sure, whether it really does not require bist U-Boot, as I has no serial console access and can't check the log. So sorry for disappointment if it will not work as described. Report me and I will delete attachment.

(Patch to original U-Boot source will be provided soon, if it really will work; just let me day or two to tidy up that mess of impulsive edits.)
That is effing awesome! I was dreaming about doing that "someday". It must have taken significant effort to add in the fastboot part of bist and then "condense" it down to just the essential parts to boot fastboot.

Thanks. This will certainly help those who erased their u-boot bist from mmc. I can't wait to test this out (but not now).

Be sure to put it in the Tools and K5 indexes...

Again, Thanks! Max karma to you for this post (when it will let me give you some again).

EDIT: I announced your tool in the simple debricking first post. I hope you do not mind hot pink.

EDIT2: I plan to replace the fastboot.bin in the MfgTool package in the Select Boot thread with this fastboot.bin, after I test it and make sure that it works correctly on both K4 and K5. Meanwhile, those who need it can do that themselves. But I prefer using the imx_usb_loader tool these days instead of MfgTool, so I can use only linux on my host PC.

Last edited by geekmaster; 10-20-2012 at 09:24 AM.
geekmaster is offline   Reply With Quote
Old 10-20-2012, 09:27 AM   #730
ixtab
(offline)
ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.ixtab ought to be getting tired of karma fortunes by now.
 
ixtab's Avatar
 
Posts: 2,903
Karma: 6677557
Join Date: Dec 2011
Device: K3, K4, K5, KPW, KPW2
Quote:
Originally Posted by eureka View Post
With the help of hammer, chisel and pile of damns I've managed to make oridinary U-Boot that includes fastboot "server", automatically goes straight into fastboot mode on booting and could be loaded with imx_usb_loader. I've used Yifan Lu's fastboot client to get idme var and it worked. And I have no desire to overwrite my partitions now Note, that check command will not return real result (as crc32 checking function was removed to decrease file size).

Of course, I can't say for sure, whether it really does not require bist U-Boot, as I has no serial console access and can't check the log. So sorry for disappointment if it will not work as described. Report me and I will delete attachment.

(Patch to original U-Boot source will be provided soon, if it really will work; just let me day or two to tidy up that mess of impulsive edits.)
GREAT!

I was trying to do that as well, but miserably failed - good to see that you succeeded and got it to work... really interested in that diff.
ixtab is offline   Reply With Quote
Old 10-20-2012, 09:36 AM   #731
geekmaster
Всё гениальное просто.
geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.
 
geekmaster's Avatar
 
Posts: 5,070
Karma: 6789001
Join Date: Nov 2011
Location: Щедрость не имеет пределов.
Device: *.*
I replaced fastboot.bin in my local copy of the Select Boot package with eureka's new fastboot.bin. MfgTool was able to start fastboot mode. The linux fastboot tool was able to do "sudo ./fastboot getvar serial" and it showed my kindle serial number.

I was not able (yet) to determine whether it was running fastboot protocol from eureka's u-boot, or if it loaded fastboot from the mmc (the old way). I suppose that I actually need to sacrifice a K5 (and a K4) by erasing mmc to properly test whether this new u-boot is up to the challenge of recovering a kindle in such a sorry state of affairs.

Also, we need to test other functions in the new fastboot.bin, to make sure that it flashes the correct locations and lengths in the mmc.

EDIT: Even with a few spare K4 and K5 demo kindles, I am (more than) hesitant to erase the mmc in them.

Last edited by geekmaster; 10-20-2012 at 09:58 AM.
geekmaster is offline   Reply With Quote
Old 10-20-2012, 09:46 AM   #732
geekmaster
Всё гениальное просто.
geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.
 
geekmaster's Avatar
 
Posts: 5,070
Karma: 6789001
Join Date: Nov 2011
Location: Щедрость не имеет пределов.
Device: *.*
This PM really needs to be public, so it can help others, and so that others can help:
Quote:
Originally Posted by adi23
Quote:
Originally Posted by geekmaster
Quote:
Originally Posted by adi23
Quote:
Originally Posted by geekmaster
Here is an image of the first 32MB of my K5 (firmware 5.0.4):
http://www.mediafire.com/?pv5s2v33ssu2ucv

At various offsets and lengths, it contains uboot and uboot-bist, and the main and diags kernels.

I suppose you could just flash the whole thing starting at offset zero (with dd), but it could potentially zero your idme vars, so be sure to rewrite them with idme before rebooting...

Or better, figure out the length and offset to the uboot-bist portion and just flash that. Be sure to read ixtab's README for flashing diags+ssh (including diags kernel) using dd instead of fastboot. Adapt for uboot offset and length instead of the kernel shown in his example...
This is my last mail received from you. I had my message box full.

I don't think i can flash through ssh becouse it's not installed. I have posted more details on Simple debricking method for K5-Touch, K4-Mini, & K3-Keyboard thread.
There is now a u-boot (non-bist) that can be loaded with MfgTool or the new command-line usb downloader tool, which has fastboot built-in. Awesome! You can thank eureka for that.
Yes i have already tryed and it works to fastboot (i will post later to thanks eureka) i have flashed both kernels and partition main and diags. Now i am able to enter diags and linux promt, but the main still have some errors. When i boott to main i receive :


kinit: do_mounts
kinit: name_to_dev_t(/dev/mmcblk0p1) = dev(179,1)
kinit: root_dev = dev(179,1)
kinit: /dev/root appears to be a ext3 filesystem
kinit: trying to mount /dev/root on /root with type ext3
kinit: Mounted root (ext3 filesystem) readonly.
EXT3-fs error (device mmcblk0p1): ext3_lookup: deleted inode referenced: 7132
/sbin/init.exe: error while loading shared libraries: libdbus-1.so.3: cannot open shared object file: Input/output error
Kernel panic - not syncing: Attempted to kill init!
Did you flash main from diags ssh with dd? If you used fastboot, it did not write the complete main partition... fastboot has a size limit and quits early while falsely reporting "success"... Use dd instead.
geekmaster is offline   Reply With Quote
Old 10-20-2012, 09:54 AM   #733
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by geekmaster View Post
I was not able (yet) to determine whether it was running fastboot protocol from eureka's u-boot, or from if it loaded fastboot from the mmc (the old way). I suppose that I actually need to sacrifice a K5 (and a K4) by erasing mmc to properly test whether this new u-boot is up to the challenge of recovering a kindle in such a sorry state of affairs.
If you have KT with access to serial console then comparison of logs of loading process of "my" fastboot.bin and "your" fastboot.bin can also throw some light on this question.
eureka is offline   Reply With Quote
Old 10-20-2012, 10:02 AM   #734
geekmaster
Всё гениальное просто.
geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.geekmaster ought to be getting tired of karma fortunes by now.
 
geekmaster's Avatar
 
Posts: 5,070
Karma: 6789001
Join Date: Nov 2011
Location: Щедрость не имеет пределов.
Device: *.*
Another PM relevant to this thread:
Quote:
Originally Posted by adi23
Quote:
Originally Posted by geekmaster
Did you flash main from diags ssh with dd? If you used fastboot, it did not write the complete main partition... fastboot has a size limit and quits early while falsely reporting "success"... Use dd instead.
Yes, i used the fastboot to flash it (forgot that it has a limit) now i just need to search how i do the flash with ssh (never used ssh)
Please continue this in the simple debricking thread. I am copying these posts there. This discussion can help others, and others can help here too.

NOTE: It appears that eureka's standalone fastboot actually did work, and adi23 is close to debricking his "erased mmc" K5 (after he flashes main with dd instead of fastboot).
geekmaster is offline   Reply With Quote
Old 10-20-2012, 10:49 AM   #735
eureka
but forgot what it's like
eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.eureka ought to be getting tired of karma fortunes by now.
 
Posts: 728
Karma: 2314258
Join Date: Dec 2011
Location: north (by northwest)
Device: Kindle Touch
Quote:
Originally Posted by eureka View Post
(Patch to original U-Boot source will be provided soon, if it really will work; just let me day or two to tidy up that mess of impulsive edits.)
Quote:
Originally Posted by geekmaster View Post
It appears that eureka's standalone fastboot actually did work, and adi23 is close to debricking his "erased mmc" K5 (after he flashes main with dd instead of fastboot).
OK, as it works and diff of changes isn't so big as I've imagined it, I post diff [to unpacked uboot_2009.08.tar.gz from Kindle_src_5.1.2_1679530004.tar.gz] as promised (I didn't clean it, though).

Version 2 (current version, it's sufficient to apply it only):
Spoiler:
PHP Code:
diff -ur uboot_original/board/freescale/mx50_arm2/mx50_arm2.c uboot_fastboot/board/freescale/mx50_arm2/mx50_arm2.c
--- uboot_original/board/freescale/mx50_arm2/mx50_arm2.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/board/freescale/mx50_arm2/mx50_arm2.c    2012-10-19 18:01:50.000000000 +0000
@@ -601,+601,@@
     
gd->bd->bi_boot_params PHYS_SDRAM_1 0x100;
 
     
/* iomux for uart */
-    setup_uart();
+    
/* setup_uart(); */
 
 #ifdef CONFIG_MXC_FEC
     /* iomux for fec */
diff -ur uboot_original/board/imx50_yoshi/config.mk uboot_fastboot/board/imx50_yoshi/config.mk
--- uboot_original/board/imx50_yoshi/config.mk    2010-11-30 23:30:43.000000000 +0000
+++ uboot_fastboot/board/imx50_yoshi/config.mk    2012-10-20 08:23:07.000000000 +0000
@@ -1,+1,@@
 
ifeq ($(TYPE),prod)
 
LDSCRIPT := $(SRCTREE)/board/$(VENDOR)/$(BOARD)/u-boot.lds
 
-TEXT_BASE 0xF8007000
+TEXT_BASE 0xF8006000
 
else
 
LDSCRIPT := $(SRCTREE)/board/$(VENDOR)/$(BOARD)/bist.lds
 
diff 
-ur uboot_original/board/imx50_yoshi/imx50_yoshi.c uboot_fastboot/board/imx50_yoshi/imx50_yoshi.c
--- uboot_original/board/imx50_yoshi/imx50_yoshi.c    2012-03-13 23:53:41.000000000 +0000
+++ uboot_fastboot/board/imx50_yoshi/imx50_yoshi.c    2013-12-14 15:14:34.000000000 +0000
@@ -64,+64,@@
 
#include <pmic.h>
 #endif
 
+#include <usb/fastboot.h>
+
 
DECLARE_GLOBAL_DATA_PTR;
 
 
unsigned int g_uart_addr UART1_BASE_ADDR;
@@ -
884,+886,@@
     return 
0;
 }
 
+
#if 0
 
inline int check_boot_mode(void
 {
     
char boot_mode[20];
@@ -
948,+951,@@
 
     return 
0;
 }
+
#endif
 
 
void board_power_off(void
 {
@@ -
1057,+1061,@@
 
#endif    //CONFIG_PMIC
 
     /* figure out which partition to boot */
-    check_boot_mode();
+    
//check_boot_mode();
+  fastboot_enable(CONFIG_MMC_BOOTFLASHFASTBOOT_USE_DEFAULT);
 
     return 
0;
 }
diff -ur uboot_original/common/cmd_bootm.c uboot_fastboot/common/cmd_bootm.c
--- uboot_original/common/cmd_bootm.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/common/cmd_bootm.c    2013-12-14 15:51:17.000000000 +0000
@@ -102,+102,@@
 
typedef int boot_os_fn (int flagint argcchar *argv[],
             
bootm_headers_t *images); /* pointers to os/initrd/fdt */
 
-#define CONFIG_BOOTM_LINUX 1
+//#define CONFIG_BOOTM_LINUX 1
 //#define CONFIG_BOOTM_NETBSD 1
 //#define CONFIG_BOOTM_RTEMS 1
 
@@ -967,+967,@@
     return (
void *)img_addr;
 }
 
+
#if 0
 
U_BOOT_CMD(
     
bootm,    CONFIG_SYS_MAXARGS,    1,    do_bootm,
     
"boot application image from memory",
@@ -
1004,+1005,@@
     
"\tprep    - OS specific prep before relocation or go\n"
     "\tgo      - start OS"
 
);
+
#endif
 
 /*******************************************************************/
 /* bootd - boot default image */
diff -ur uboot_original/common/cmd_gadget.c uboot_fastboot/common/cmd_gadget.c
--- uboot_original/common/cmd_gadget.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/common/cmd_gadget.c    2013-12-14 16:02:22.000000000 +0000
@@ -25,+25,@@
 
#include <common.h>
 #include <command.h>
 
+#if 0
 #ifdef CONFIG_GADGET_FASTBOOT
 #include <usb/fastboot.h>
 
@@ -52,+53,@@
     
"Fastboot",
     
"fastboot");
 
#endif
+#endif
 
 #ifdef CONFIG_GADGET_FILE_STORAGE
 #include <usb/file_storage.h>
diff -ur uboot_original/common/cmd_nvedit.c uboot_fastboot/common/cmd_nvedit.c
--- uboot_original/common/cmd_nvedit.c    2010-07-13 16:06:35.000000000 +0000
+++ uboot_fastboot/common/cmd_nvedit.c    2013-12-14 16:23:35.000000000 +0000
@@ -172,+172,@@
 
 
int _do_setenv (int flagint argcchar *argv[])
 {
+
#if 0
     
int   ilenoldval;
     
int   console = -1;
     
uchar *env, *nxt NULL;
@@ -
395,15 +396,18 @@
 
#endif    /* CONFIG_AMIGAONEG3SE */
 
     
return 0;
+
#endif
 
}
 
 
int setenv (char *varnamechar *varvalue)
 {
+
#if 0
     
char *argv[4] = { "setenv"varnamevarvalueNULL };
     if (
varvalue == NULL)
         return 
_do_setenv (02argv);
     else
         return 
_do_setenv (03argv);
+
#endif
 
}
 
 
#ifdef CONFIG_HAS_UID
@@ -416,12 +420,14 @@
 
 
int do_setenv (cmd_tbl_t *cmdtpint flagint argcchar *argv[])
 {
+
#if 0
     
if (argc 2) {
         
cmd_usage(cmdtp);
         return 
1;
     }
 
     return 
_do_setenv (flagargcargv);
+
#endif
 
}
 
 
/************************************************************************
@@ -596,6 +602,7 @@
 
 /**************************************************/
 
+#if 0
 
U_BOOT_CMD(
     
printenvCONFIG_SYS_MAXARGS1,    do_printenv,
     
"print environment variables",
@@ -
639,+646,@@
     
"    - run the commands in the environment variable(s) 'var'"
 
);
 
#endif
+#endif
diff -ur uboot_original/common/main.c uboot_fastboot/common/main.c
--- uboot_original/common/main.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/common/main.c    2013-12-14 16:21:02.000000000 +0000
@@ -273,+273,@@
 
 
void main_loop (void)
 {
+
#if 0
 #ifndef CONFIG_SYS_HUSH_PARSER
     
static char lastcommand[CONFIG_SYS_CBSIZE] = { 0, };
     
int len;
@@ -
512,+513,@@
         }
     }
 
#endif /*CONFIG_SYS_HUSH_PARSER*/
+#endif
 
}
 
 
#ifdef CONFIG_BOOT_RETRY_TIME
@@ -973,+975,@@
 
 
int readline_into_buffer (const char *const promptchar buffer)
 {
+
#if 0
     
char *buffer;
 
#ifdef CONFIG_CMDLINE_EDITING
     
unsigned int len=MAX_CMDBUF_SIZE;
@@ -
1096,+1099,@@
 
#ifdef CONFIG_CMDLINE_EDITING
     
}
 
#endif
+#endif
 
}
 
 
/****************************************************************************/
@@ -1311,+1315,@@
 
 
int run_command (const char *cmdint flag)
 {
+
#if 0
     
cmd_tbl_t *cmdtp;
     
char cmdbuf[CONFIG_SYS_CBSIZE];    /* working copy of cmd        */
     
char *token;            /* start of token in cmdbuf    */
@@ -1432,+1437,@@
     }
 
     return 
rc rc repeatable;
+
#endif
 
}
 
 
/****************************************************************************/
diff -ur uboot_original/drivers/usb/gadget/fastboot.c uboot_fastboot/drivers/usb/gadget/fastboot.c
--- uboot_original/drivers/usb/gadget/fastboot.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/drivers/usb/gadget/fastboot.c    2012-10-19 17:41:45.000000000 +0000
@@ -630,+630,@@
 
extern void board_reset(void);
 
extern void board_power_off(void);
 
extern unsigned int get_dram_size(void);
-
extern int mmc_crc32_test (uint partuint startint sizeuint crc);
+
/*extern int mmc_crc32_test (uint part, uint start, int size, uint crc);*/
 
extern int do_pass (cmd_tbl_t *cmdtpint flagint argcchar *argv[]);
 
extern int do_fail (cmd_tbl_t *cmdtpint flagint argcchar *argv[]);
 
@@ -
1030,10 +1030,10 @@
         
src = (unsigned char *) strtok(NULL" \0"); // get crc
         
crc = (uint)simple_strtoul((char *)srcNULL16);
 
-        if (
mmc_crc32_test(part_indexstartsizecrc)) {
+        
/*if (mmc_crc32_test(part_index, start, size, crc)) {
             fastboot_send_reply("FAILcrc failure");
             goto out;
-        }
+        }*/
 
         
fastboot_send_reply("OKAY");
     }
diff -ur uboot_original/include/configs/imx50_yoshi.h uboot_fastboot/include/configs/imx50_yoshi.h
--- uboot_original/include/configs/imx50_yoshi.h    2012-03-14 17:14:23.000000000 +0000
+++ uboot_fastboot/include/configs/imx50_yoshi.h    2013-12-14 15:25:11.000000000 +0000
@@ -41,+41,@@
 
#define CONFIG_SYS_AXIA_PODF    0
 #define CONFIG_SYS_AXIB_PODF    1
 
-#define CONFIG_DISPLAY_CPUINFO
-#define CONFIG_DISPLAY_BOARDINFO
+//#define CONFIG_DISPLAY_CPUINFO
+//#define CONFIG_DISPLAY_BOARDINFO
 
 #define CONFIG_SYS_64BIT_VSPRINTF
 
@@ -87,+87,18 @@
 
#define CONFIG_MX50_GPIO    1
 
 /*
+ * SPI Configs
+ */
+#define CONFIG_IMX_SPI
+#define CONFIG_IMX_CSPI
+#define CONFIG_IMX_ECSPI
+#define MAX_SPI_BYTES        (8 * 4)
+#define CONFIG_IMX_SPI_PMIC_BUS 3
+#define CONFIG_IMX_SPI_PMIC_CS    0
+#define CONFIG_PMIC        1
+#define CONFIG_PMIC_13892    1
+
+
/*
  * MMC Configs
  */
 #define CONFIG_MMC            1
@@ -107,+119,23 @@
 
#define CONFIG_BOOT_PARTITION_ACCESS
 #define CONFIG_BOOT_FROM_PARTITION    1
 
+#define CONFIG_MMC_MAX_TRANSFER_SIZE    (0xFFFF * 512)
+/*
+ * USB Configs
+ */
+#define CONFIG_USB_DEVICE        1
+#define CONFIG_DRIVER_FSLUSB        1
+#define CONFIG_GADGET_FASTBOOT        1
+
+
#define CONFIG_USBD_MANUFACTURER "Amazon"
+#define CONFIG_USBD_PRODUCT_NAME "Kindle"
+
+
#define CONFIG_USBD_VENDORID            0x1949
+#define CONFIG_USBD_PRODUCTID_FASTBOOT        0xd0d0
+#define CONFIG_FASTBOOT_MAX_DOWNLOAD_LEN    ((get_dram_size()) - (2*1024*1024) - (CONFIG_FASTBOOT_TEMP_BUFFER - CONFIG_SYS_SDRAM_BASE))
+#define CONFIG_FASTBOOT_TEMP_BUFFER        0x7A000000
+//#define CONFIG_CMD_GADGET 1
+
 
#define CONFIG_BOOT_HALT_VOLTAGE    3400    /* 3.4V */
 #define CONFIG_BOOT_CONTINUE_VOLTAGE    3600    /* 3.6V */    
 #define CONFIG_BOOT_AUTOCHG_VOLTAGE    3800    /* 3.8V */    
@@ -121,15 +150,15 @@
  * 
Command definition
  
***********************************************************/
 
-
#define CONFIG_CMD_BOOTD    /* bootd            */
-#define CONFIG_CMD_RUN        /* run command in env variable    */
-#define CONFIG_CMD_LOG
+//#define CONFIG_CMD_BOOTD    /* bootd            */
+//#define CONFIG_CMD_RUN        /* run command in env variable    */
+//#define CONFIG_CMD_LOG
 
 /* Lab 126 cmds */
-#define CONFIG_CMD_BIST        1
-#define CONFIG_CMD_PMIC        1
+//#define CONFIG_CMD_BIST        1
+//#define CONFIG_CMD_PMIC        1
 #define CONFIG_CMD_IDME        1
-#define CONFIG_CMD_HALT        1
+//#define CONFIG_CMD_HALT        1
 
 #define CONFIG_IDME_UPDATE        1
 #define CONFIG_IDME_UPDATE_ADDR        0x3f000
@@ -154,+183,@@
 
#endif
 
 #define CONFIG_LOADADDR        0x70800000    /* loadaddr env var */
-#define CONFIG_RD_LOADADDR    (CONFIG_LOADADDR + 0x300000)
+/*#define CONFIG_RD_LOADADDR    (CONFIG_LOADADDR + 0x300000)
 #define CONFIG_BISTADDR        0x79800000
 
 #define CONFIG_BISTCMD_LOCATION (CONFIG_BISTADDR - 0x80000)
@@ -168,7 +197,7 @@
     "bootargs_diags=setenv bootargs consoleblank=0 rootwait ro ip=off root=/dev/mmcblk0p2 quiet eink=fslepdc\0" \
     "bootcmd_diags=run bootargs_diags ; bootm " MK_STR(CONFIG_MMC_BOOTDIAGS_ADDR) "\0" \
     "bootcmd_factory=bist halt\0" \
-    "bootcmd_fastboot=bist fastboot\0"
+    "bootcmd_fastboot=bist fastboot\0"*/
 
 /*
  * Miscellaneous configurable options
@@ -190,7 +219,7 @@
 #define CONFIG_WDOG_PRINTK_SIZE        (4096 * 2)
 #define CONFIG_SYS_MEMTEST_END      (PHYS_SDRAM_1 + get_dram_size() - 1 - CONFIG_WDOG_PRINTK_SIZE)
 
-#define CONFIG_LOGBUFFER
+//#define CONFIG_LOGBUFFER
 
 #define CONFIG_POST         (CONFIG_SYS_POST_MEMORY | \
                              CONFIG_SYS_POST_FAIL)
@@ -201,7 +230,7 @@
 
 #define CONFIG_SYS_HZ                1000
 
-#define CONFIG_CMDLINE_EDITING    1
+//#define CONFIG_CMDLINE_EDITING    1
 
 /*-----------------------------------------------------------------------
  * Physical Memory Map 

Original (old) version:
Spoiler:
This (initial) version didn't contain code required to reboot whole board, so fastboot reboot command didn't fully work.
PHP Code:
diff -ur uboot/board/imx50_yoshi/config.mk uboot_fastboot/board/imx50_yoshi/config.mk
--- uboot/board/imx50_yoshi/config.mk    2010-11-30 23:30:43.000000000 +0000
+++ uboot_fastboot/board/imx50_yoshi/config.mk    2012-10-20 08:23:07.000000000 +0000
@@ -1,+1,@@
 
ifeq ($(TYPE),prod)
 
LDSCRIPT := $(SRCTREE)/board/$(VENDOR)/$(BOARD)/u-boot.lds
 
-TEXT_BASE 0xF8007000
+TEXT_BASE 0xF8006000
 
else
 
LDSCRIPT := $(SRCTREE)/board/$(VENDOR)/$(BOARD)/bist.lds
 
diff 
-ur uboot/board/imx50_yoshi/imx50_yoshi.c uboot_fastboot/board/imx50_yoshi/imx50_yoshi.c
--- uboot/board/imx50_yoshi/imx50_yoshi.c    2012-03-13 23:53:41.000000000 +0000
+++ uboot_fastboot/board/imx50_yoshi/imx50_yoshi.c    2012-10-19 18:42:52.000000000 +0000
@@ -889,+889,10 @@
     
char boot_mode[20];
     
char boot_cmd[20];
 
+    
setenv("bootcmd""fastboot");
+
+    return 
0;
+
 
#ifdef CONFIG_BIST
     
setenv("bootdelay""-1");
 
#endif
diff -ur uboot/common/cmd_bootm.c uboot_fastboot/common/cmd_bootm.c
--- uboot/common/cmd_bootm.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/common/cmd_bootm.c    2012-10-19 20:24:16.000000000 +0000
@@ -102,+102,@@
 
typedef int boot_os_fn (int flagint argcchar *argv[],
             
bootm_headers_t *images); /* pointers to os/initrd/fdt */
 
-#define CONFIG_BOOTM_LINUX 1
+//#define CONFIG_BOOTM_LINUX 1
 //#define CONFIG_BOOTM_NETBSD 1
 //#define CONFIG_BOOTM_RTEMS 1
 
diff -ur uboot/drivers/usb/gadget/fastboot.c uboot_fastboot/drivers/usb/gadget/fastboot.c
--- uboot/drivers/usb/gadget/fastboot.c    2012-03-14 17:14:22.000000000 +0000
+++ uboot_fastboot/drivers/usb/gadget/fastboot.c    2012-10-19 17:41:45.000000000 +0000
@@ -630,+630,@@
 
extern void board_reset(void);
 
extern void board_power_off(void);
 
extern unsigned int get_dram_size(void);
-
extern int mmc_crc32_test (uint partuint startint sizeuint crc);
+
/*extern int mmc_crc32_test (uint part, uint start, int size, uint crc);*/
 
extern int do_pass (cmd_tbl_t *cmdtpint flagint argcchar *argv[]);
 
extern int do_fail (cmd_tbl_t *cmdtpint flagint argcchar *argv[]);
 
@@ -
1030,10 +1030,10 @@
         
src = (unsigned char *) strtok(NULL" \0"); // get crc
         
crc = (uint)simple_strtoul((char *)srcNULL16);
 
-        if (
mmc_crc32_test(part_indexstartsizecrc)) {
+        
/*if (mmc_crc32_test(part_index, start, size, crc)) {
             fastboot_send_reply("FAILcrc failure");
             goto out;
-        }
+        }*/
 
         
fastboot_send_reply("OKAY");
     }
diff -ur uboot/include/configs/imx50_yoshi.h uboot_fastboot/include/configs/imx50_yoshi.h
--- uboot/include/configs/imx50_yoshi.h    2012-03-14 17:14:23.000000000 +0000
+++ uboot_fastboot/include/configs/imx50_yoshi.h    2012-10-20 14:39:38.000000000 +0000
@@ -41,+41,@@
 
#define CONFIG_SYS_AXIA_PODF    0
 #define CONFIG_SYS_AXIB_PODF    1
 
-#define CONFIG_DISPLAY_CPUINFO
-#define CONFIG_DISPLAY_BOARDINFO
+//#define CONFIG_DISPLAY_CPUINFO
+//#define CONFIG_DISPLAY_BOARDINFO
 
 #define CONFIG_SYS_64BIT_VSPRINTF
 
@@ -107,+107,23 @@
 
#define CONFIG_BOOT_PARTITION_ACCESS
 #define CONFIG_BOOT_FROM_PARTITION    1
 
+#define CONFIG_MMC_MAX_TRANSFER_SIZE    (0xFFFF * 512)
+/*
+ * USB Configs
+ */
+#define CONFIG_USB_DEVICE        1
+#define CONFIG_DRIVER_FSLUSB        1
+#define CONFIG_GADGET_FASTBOOT        1
+
+
#define CONFIG_USBD_MANUFACTURER "Amazon"
+#define CONFIG_USBD_PRODUCT_NAME "Kindle"
+
+
#define CONFIG_USBD_VENDORID            0x1949
+#define CONFIG_USBD_PRODUCTID_FASTBOOT        0xd0d0
+#define CONFIG_FASTBOOT_MAX_DOWNLOAD_LEN    ((get_dram_size()) - (2*1024*1024) - (CONFIG_FASTBOOT_TEMP_BUFFER - CONFIG_SYS_SDRAM_BASE))
+#define CONFIG_FASTBOOT_TEMP_BUFFER        0x7A000000
+#define CONFIG_CMD_GADGET 1
+
 
#define CONFIG_BOOT_HALT_VOLTAGE    3400    /* 3.4V */
 #define CONFIG_BOOT_CONTINUE_VOLTAGE    3600    /* 3.6V */    
 #define CONFIG_BOOT_AUTOCHG_VOLTAGE    3800    /* 3.8V */    
@@ -121,15 +138,15 @@
  * 
Command definition
  
***********************************************************/
 
-
#define CONFIG_CMD_BOOTD    /* bootd            */
-#define CONFIG_CMD_RUN        /* run command in env variable    */
-#define CONFIG_CMD_LOG
+//#define CONFIG_CMD_BOOTD    /* bootd            */
+//#define CONFIG_CMD_RUN        /* run command in env variable    */
+//#define CONFIG_CMD_LOG
 
 /* Lab 126 cmds */
-#define CONFIG_CMD_BIST        1
-#define CONFIG_CMD_PMIC        1
+//#define CONFIG_CMD_BIST        1
+//#define CONFIG_CMD_PMIC        1
 #define CONFIG_CMD_IDME        1
-#define CONFIG_CMD_HALT        1
+//#define CONFIG_CMD_HALT        1
 
 #define CONFIG_IDME_UPDATE        1
 #define CONFIG_IDME_UPDATE_ADDR        0x3f000
@@ -190,+207,@@
 
#define CONFIG_WDOG_PRINTK_SIZE        (4096 * 2)
 #define CONFIG_SYS_MEMTEST_END      (PHYS_SDRAM_1 + get_dram_size() - 1 - CONFIG_WDOG_PRINTK_SIZE)
 
-#define CONFIG_LOGBUFFER
+//#define CONFIG_LOGBUFFER
 
 #define CONFIG_POST         (CONFIG_SYS_POST_MEMORY | \
                              
CONFIG_SYS_POST_FAIL)
@@ -
201,+218,@@
 
 
#define CONFIG_SYS_HZ                1000
 
-#define CONFIG_CMDLINE_EDITING    1
+//#define CONFIG_CMDLINE_EDITING    1
 
 /*-----------------------------------------------------------------------
  * Physical Memory Map 

Last edited by eureka; 12-22-2013 at 12:31 PM. Reason: add second version of diff
eureka is offline   Reply With Quote
Reply

Tags
debricking

Thread Tools Search this Thread
Search this Thread:

Advanced Search

Forum Jump

Similar Threads
Thread Thread Starter Forum Replies Last Post
Which one Nook simple touch or Kobo mini? capuchino71 Which one should I buy? 18 07-12-2013 05:09 PM
Sell Kindle Keyboard 3G, Nook Simple Touch austinmitchell Flea Market 5 03-01-2013 11:34 AM
I have some questions about K4 touch debricking drjonvargas Kindle Developer's Corner 4 04-22-2012 03:46 PM
kindle touch simple debricking for help non_fox Amazon Kindle 4 04-18-2012 08:32 PM
Troubleshooting simple kindle touch (and k4nt) debricking method geekmaster Amazon Kindle 0 03-02-2012 10:31 PM


All times are GMT -4. The time now is 01:42 PM.


MobileRead.com is a privately owned, operated and funded community.